通过

_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_acq(
   __int64 *a,
   __int64 b
);
unsigned char _interlockedbittestandreset64_nf(
   __int64 *a,
   __int64 b
);
unsigned char _interlockedbittestandreset64_rel(
   __int64 *a,
   __int64 b
);
unsigned char _interlockedbittestandreset64_HLEAcquire(
   __int64 *a,
   __int64 b
);
unsigned char _interlockedbittestandreset64_HLERelease(
   __int64 *a,
   __int64 b
);

参数

a
[in] 指向要检查的内存的指针。

b
[in] 要测试的位位置。

返回值

由 b 指定的位置上的位的原始值。

要求

Intrinsic 体系结构 头文件
_interlockedbittestandreset x86、ARM、x64、ARM64 <intrin.h>
.- . ARM、ARM64 <intrin.h>
.- . ARM64 <intrin.h>
%> x86、x64 <immintrin.h>
_interlockedbittestandreset64 x64、ARM64 <intrin.h>
%> x64 <immintrin.h>

备注

在 x86 和 x64 处理器上，这些内部函数使用 lock btr 指令在原子操作中读取指定的位并将其设置为零。

在 ARM 处理器上，使用带 _acq 和 _rel 后缀的内部函数（例如在临界区的起点和结尾处）获取和发布语义。 带 _nf（“无围墙”）后缀的 ARM 内部函数不能充当内存屏障。

在支持硬件锁省略 (HLE) 指令的 Intel 处理器上，带 _HLEAcquire 和 _HLERelease 后缀的内部函数包括一条发送到处理器的提示，可通过消除硬件中的锁写步骤加快速度。 如果在不支持 HLE 的处理器上调用这些内部函数，则忽略此提示。

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

结束 Microsoft 专用

另请参阅

编译器内部函数
与 x86 编译器冲突