_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_HLEAcquire(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandset64_HLERelease(
__int64 *a,
__int64 b
);
參數
[in] a
要檢查的記憶體指標。[in] b
要測試的位元位置。
傳回值
設定之前位置 b 的位元值。
需求
內建 |
架構 |
頁首 |
---|---|---|
_interlockedbittestandset |
x86、ARM、x64 |
<intrin.h> |
_interlockedbittestandset_acq, _interlockedbittestandset_nf, _interlockedbittestandset_rel |
ARM |
<intrin.h> |
_interlockedbittestandset_HLEAcquire, _interlockedbittestandset_HLERelease |
x86、x64 |
<immintrin.h> |
_interlockedbittestandset64 |
x64 |
<intrin.h> |
_interlockedbittestandset64_HLEAcquire, _interlockedbittestandset64_HLERelease |
x64 |
<immintrin.h> |
備註
在 x86 和 x64 處理器上,這些內建函式會使用 lock bts 指令讀取,並將指定的位元設為 1。 此作業是不可部分完成的。
在 ARM 處理器上,搭配取得和釋放語意的 _acq 和 _rel 字尾使用內建函式,例如在重要區段的開頭和結尾處。 搭配 _nf (「無範圍」) 字尾的 ARM 內建函式不會當做記憶體屏障。
在支援 Hardware Lock Elision (HLE) 指令的 Intel 處理器上,搭配 _HLEAcquire 和 _HLERelease 字尾的內建函式會包含對處理器的提示,提示其可以藉由消除硬體中鎖定寫入 (lock write) 的階段以加速效能。 如果這些內建函式在不支援 HLE 的處理器上被呼叫,則會忽略提示。
這些常式只可做為內建函式。