Microsoft 专用
生成一个指令,该指令将地址 a 的位 b 设置为零并返回其原始值。
unsigned char _interlockedbittestandreset(
long *a,
long b
);
unsigned char _interlockedbittestandreset_acq(
long *a,
long b
);
unsigned char _interlockedbittestandreset_HLEAcquire(
long *a,
long b
);
unsigned char _interlockedbittestandreset_HLERelease(
long *a,
long b
);
unsigned char _interlockedbittestandreset_nf(
long *a,
long b
);
unsigned char _interlockedbittestandreset_rel(
long *a,
long b
);
unsigned char _interlockedbittestandreset64(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_HLEAcquire(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_HLERelease(
__int64 *a,
__int64 b
);
参数
[in] a
指向要检查的内存的指针。[in] b
要测试的位位置。
返回值
由 b 指定的位置上的位的原始值。
要求
内部函数 |
体系结构 |
Header |
---|---|---|
_interlockedbittestandreset |
x86、ARM、x64 |
<intrin.h> |
_interlockedbittestandreset_acq, _interlockedbittestandreset_nf, _interlockedbittestandreset_rel |
ARM |
<intrin.h> |
_interlockedbittestandreset_HLEAcquire, _interlockedbittestandreset_HLERelease |
x86, x64 |
<immintrin.h> |
_interlockedbittestandreset64 |
x64 |
<intrin.h> |
_interlockedbittestandreset64_HLEAcquire, _interlockedbittestandreset64_HLERelease |
x64 |
<immintrin.h> |
备注
在 x86 和 x64 处理器上,这些内部函数使用 lock btr 指令在原子操作中读取指定的位并将其设置为零。
在 ARM 处理器上,使用带 _acq 和 _rel 后缀的内部函数(例如在临界区的起点和结尾处)获取和发布语义。 带 _nf(“无围墙”)后缀的 ARM 内部函数不能充当内存屏障。
在支持硬件锁省略 (HLE) 指令的 Intel 处理器上,带 _HLEAcquire 和 _HLERelease 后缀的内部函数包括一条发送到处理器的提示,可通过消除硬件中的锁写步骤加快速度。 如果在不支持 HLE 的处理器上调用这些函数,则忽略此提示。
这些例程只能用作内部函数。