_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>
_interlockedbittestandset_acq, _interlockedbittestandset_nf, _interlockedbittestandset_rel	ARM、ARM64	<intrin.h>
_interlockedbittestandset64_acq, _interlockedbittestandset64_nf, _interlockedbittestandset64_rel	ARM64	<intrin.h>
_interlockedbittestandset_HLEAcquire，_interlockedbittestandset_HLERelease	x86、x64	<immintrin.h>
_interlockedbittestandset64	x64、ARM64	<intrin.h>
_interlockedbittestandset64_HLEAcquire，_interlockedbittestandset64_HLERelease	x64	<immintrin.h>

注解

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

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

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

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

结束 Microsoft 专用

另请参阅

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