_interlockedbittestandset 内部函数
Microsoft 专用
生成可以检查地址 a
的位 b
的指令,返回其当前值,然后将位设置为 1。
语法
unsigned char _interlockedbittestandset(
long *a,
long b
);
unsigned char _interlockedbittestandset_acq(
long *a,
long b
);
unsigned char _interlockedbittestandset_HLEAcquire(
long *a,
long b
);
unsigned char _interlockedbittestandset_HLERelease(
long *a,
long b
);
unsigned char _interlockedbittestandset_nf(
long *a,
long b
);
unsigned char _interlockedbittestandset_rel(
long *a,
long b
);
unsigned char _interlockedbittestandset64(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandset64_acq(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandset64_nf(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandset64_rel(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandset64_HLEAcquire(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandset64_HLERelease(
__int64 *a,
__int64 b
);
参数
a
[in] 指向要检查的内存的指针。
b
[in] 要测试的位位置。
返回值
在位置 b
上的位在其设置前的值。
要求
Intrinsic | 体系结构 | 头文件 |
---|---|---|
_interlockedbittestandset |
x86、ARM、x64、ARM64 | <intrin.h> |
.- . | ARM、ARM64 | <intrin.h> |
.- . | ARM64 | <intrin.h> |
%> | x86、x64 | <immintrin.h> |
_interlockedbittestandset64 |
x64、ARM64 | <intrin.h> |
%> | x64 | <immintrin.h> |
注解
在 x86 和 x64 处理器上,这些内部函数使用 lock bts
指令读取指定的位并将其设置为 1。 此操作为原子性操作。
在 ARM 和 ARM64 处理器上,使用带 _acq
和 _rel
后缀的内部函数(例如在临界区的起点和结尾处)获取和发布语义。 带 _nf
(“无围墙”)后缀的 ARM 内部函数不能充当内存屏障。
在支持硬件锁省略 (HLE) 指令的 Intel 处理器上,带 _HLEAcquire
和 _HLERelease
后缀的内部函数包括一条发送到处理器的提示,可通过消除硬件中的锁写步骤加快速度。 如果在不支持 HLE 的处理器上调用这些内部函数,则忽略此提示。
这些例程只能用作内部函数。
结束 Microsoft 专用