_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 值。
需求
| 內建 | 架構 | 頁首 |
|---|---|---|
_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後綴取得和釋放語意，例如在關鍵區段的開頭和結尾。 具有 （“無柵欄”） 後綴的 ARM 內部 _nf 函數不會作為記憶體屏障。
在支援 Hardware Lock Elision (HLE) 指令的 Intel 處理器上，搭配 _HLEAcquire 和 _HLERelease 字尾的內建函式會包含對處理器的提示，提示其可以藉由消除硬體中鎖定寫入 (lock write) 的階段以加速效能。 如果在不支援 HLE 的處理器上呼叫這些內部函數，則會忽略提示。
這些常式僅以內建函式的形式供您使用。
END Microsoft 特定的