_InterlockedCompareExchangePointer 内部函数

Microsoft 专用

如果 Exchange 和 Destination 地址相等，则执行原子操作，将 Comparand 地址存储在 Destination 地址中。

语法

void * _InterlockedCompareExchangePointer (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);
void * _InterlockedCompareExchangePointer_acq (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);
void * _InterlockedCompareExchangePointer_HLEAcquire (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);
void * _InterlockedCompareExchangePointer_HLERelease (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);
void * _InterlockedCompareExchangePointer_nf (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);
void * _InterlockedCompareExchangePointer_np (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);
void * _InterlockedCompareExchangePointer_rel (
   void * volatile * Destination,
   void * Exchange,
   void * Comparand
);

参数

目标
[in, out] 指向目标值的指针。 忽略此标记。

Exchange
[in] 交换指针。 忽略此标记。

Comparand
[in] 与目标值比较的指针。 忽略此标记。

返回值

返回值是目标的初始值。

要求

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

备注

_InterlockedCompareExchangePointer 执行 Destination 地址与 Comparand 地址之间的原子比较。 如果 Destination 地址与 Comparand 地址相等，则 Exchange 地址将存储在由 Destination 指定的地址中。 否则，不会执行任何操作。

_InterlockedCompareExchangePointer 对 Win32 Windows SDK InterlockedCompareExchangePointer 函数提供了编译器内部函数支持。

有关如何使用 _InterlockedCompareExchangePointer 的示例，请参阅 _InterlockedDecrement。

ARM 平台上，如果需要（例如在临界区的起点和终点）获取和发布语义，可以使用带 _acq 和 _rel 后缀的函数。 带 _nf（“无围墙”）后缀的 ARM 内部函数不能充当内存屏障。

带 _np（“无预取”）后缀的函数可以阻止编译器插入可能的预取操作。

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

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

结束 Microsoft 专用

另请参阅

编译器内部函数
关键字