_interlockedbittestandreset 内部函数

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 的处理器上调用这些函数,则忽略此提示。

这些例程只能用作内部函数。

请参见

参考

编译器内部函数

与 x86 编译器冲突