_InterlockedExchangeAdd 内部函数
Microsoft 专用
对 Win32 Windows SDK _InterlockedExchangeAdd 内部函数提供了编译器内部函数支持。
语法
long _InterlockedExchangeAdd(
long volatile * Addend,
long Value
);
long _InterlockedExchangeAdd_acq(
long volatile * Addend,
long Value
);
long _InterlockedExchangeAdd_rel(
long volatile * Addend,
long Value
);
long _InterlockedExchangeAdd_nf(
long volatile * Addend,
long Value
);
long _InterlockedExchangeAdd_HLEAcquire(
long volatile * Addend,
long Value
);
long _InterlockedExchangeAdd_HLERelease(
long volatile * Addend,
long Value
);
char _InterlockedExchangeAdd8(
char volatile * Addend,
char Value
);
char _InterlockedExchangeAdd8_acq(
char volatile * Addend,
char Value
);
char _InterlockedExchangeAdd8_rel(
char volatile * Addend,
char Value
);
char _InterlockedExchangeAdd8_nf(
char volatile * Addend,
char Value
);
short _InterlockedExchangeAdd16(
short volatile * Addend,
short Value
);
short _InterlockedExchangeAdd16_acq(
short volatile * Addend,
short Value
);
short _InterlockedExchangeAdd16_rel(
short volatile * Addend,
short Value
);
short _InterlockedExchangeAdd16_nf(
short volatile * Addend,
short Value
);
__int64 _InterlockedExchangeAdd64(
__int64 volatile * Addend,
__int64 Value
);
__int64 _InterlockedExchangeAdd64_acq(
__int64 volatile * Addend,
__int64 Value
);
__int64 _InterlockedExchangeAdd64_rel(
__int64 volatile * Addend,
__int64 Value
);
__int64 _InterlockedExchangeAdd64_nf(
__int64 volatile * Addend,
__int64 Value
);
__int64 _InterlockedExchangeAdd64_HLEAcquire(
__int64 volatile * Addend,
__int64 Value
);
__int64 _InterlockedExchangeAdd64_HLERelease(
__int64 volatile * Addend,
__int64 Value
);
参数
加数
[in, out] 要相加的值；由加法得出的结果代替。
值
[in] 要相加的值。
返回值
返回值是由 Addend 参数指向的变量的初始值。
要求
| Intrinsic | 体系结构 | Header |
|---|---|---|
| .- . | x86、ARM、x64、ARM64 | <intrin.h> |
_InterlockedExchangeAdd64 |
ARM、x64、ARM64 | <intrin.h> |
| ARM、ARM64 | <intrin.h> | |
| %> | x86、x64 | <immintrin.h> |
| %> | x64 | <immintrin.h> |
备注
_InterlockedExchangeAdd 存在几种变体，这些变体根据其涉及的数据类型和是否使用特定于处理器获取或发布语义而有所不同。
当 _InterlockedExchangeAdd 函数对 32 位整数值操作时，_InterlockedExchangeAdd8 对 8 位整数值操作，_InterlockedExchangeAdd16 对 16 位整数值操作且 _InterlockedExchangeAdd64 对 64 位整数值操作。
ARM 平台上，如果需要（例如在临界区的起点和终点）获取和发布语义，可以使用带 _acq 和 _rel 后缀的函数。 带 _nf（“no fence”）后缀的内部函数不充当内存屏障。
在支持硬件锁省略 (HLE) 指令的 Intel 平台，带 _HLEAcquire 和 _HLERelease 后缀的内部函数包括一个发送到处理器的提示，可以通过消除硬件中的锁写步骤来提升速度。 如果在不支持 HLE 的平台上调用这些内部函数，则忽略此提示。
这些例程只能用作内部函数。 即使使用 /Oi 或 #pragma intrinsic，它们也是内部函数。 对于这些内部函数，不能使用 #pragma function。
示例
有关如何使用 _InterlockedExchangeAdd 的示例，请参阅 _InterlockedDecrement。
结束 Microsoft 专用