Microsoft 专用
如果 Comparand 和 Destination 地址相等，则执行原子操作，将 Exchange 地址存储在 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 ); long _InterlockedCompareExchangePointer_rel ( void * volatile * Destination, void * Exchange, void * Comparand );
参数
[in, out] Destination
指向目标值的指针。 忽略此标记。[in] Exchange
交换指针。 忽略此标记。[in] Comparand
与目标值比较的指针。 忽略此标记。
返回值
返回值是目标的初始值。
要求
内部函数 |
体系结构 |
Header |
|---|---|---|
_InterlockedCompareExchangePointer |
x86、ARM、x64 |
<intrin.h> |
_InterlockedCompareExchangePointer_acq, _InterlockedCompareExchangePointer_nf, _InterlockedCompareExchangePointer_rel |
ARM |
<iiintrin.h> |
_InterlockedCompareExchangePointer_HLEAcquire, _InterlockedCompareExchangePointer_HLERelease |
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 的平台上调用这些函数，则忽略此提示。
这些例程只能用作内部函数。