_interlockedbittestandreset 組み込み関数
Microsoft 固有の仕様
アドレス a
のビット b
を 0 に設定し、その元の値を返す命令を生成します。
構文
unsigned char _interlockedbittestandreset(
long *a,
long b
);
unsigned char _interlockedbittestandreset_acq(
long *a,
long b
);
unsigned char _interlockedbittestandreset_HLEAcquire(
long *a,
long b
);
unsigned char _interlockedbittestandreset_HLERelease(
long *a,
long b
);
unsigned char _interlockedbittestandreset_nf(
long *a,
long b
);
unsigned char _interlockedbittestandreset_rel(
long *a,
long b
);
unsigned char _interlockedbittestandreset64(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_acq(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_nf(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_rel(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_HLEAcquire(
__int64 *a,
__int64 b
);
unsigned char _interlockedbittestandreset64_HLERelease(
__int64 *a,
__int64 b
);
パラメーター
a
[in] 検査するメモリを指すポインター。
b
[in] テストするビット位置。
戻り値
b
で指定された位置にあるビットの元の値。
要件
Intrinsic | Architecture | ヘッダー |
---|---|---|
_interlockedbittestandreset |
x86、ARM、x64、ARM64 | <intrin.h> |
_interlockedbittestandreset_acq 、 _interlockedbittestandreset_nf 、 _interlockedbittestandreset_rel |
ARM、ARM64 | <intrin.h> |
_interlockedbittestandreset64_acq 、 _interlockedbittestandreset64_nf 、 _interlockedbittestandreset64_rel |
ARM64 | <intrin.h> |
_interlockedbittestandreset_HLEAcquire , _interlockedbittestandreset_HLERelease |
x86、x64 | <immintrin.h> |
_interlockedbittestandreset64 |
x64、ARM64 | <intrin.h> |
_interlockedbittestandreset64_HLEAcquire , _interlockedbittestandreset64_HLERelease |
x64 | <immintrin.h> |
解説
x86 および x64 プロセッサでは、これらの組み込みはアトミックな演算で指定されたビットを読み込み、その値を 0 に設定する lock btr
命令を使用します。
ARM プロセッサでは、クリティカル セクションの最初と最後などでの取得と解放のセマンティクスのために、_acq
および _rel
サフィックスの付いた組み込みを使用します。 ARM の組込み関数で _nf
("no fence") のサフィックスを持つものは、メモリ バリアとして機能しません。
Hardware Lock Elision (HLE) 命令をサポートする Intel プロセッサでは、_HLEAcquire
および _HLERelease
サフィックスの付いた組み込みにプロセッサへのヒントが含まれています。このヒントによりハードウェアでのロック書き込み手順を省くことで、パフォーマンスを向上させることができます。 HLE をサポートしていないプロセッサ上でこれらの組み込みが呼び出された場合、ヒントは無視されます。
これらのルーチンは、組み込みとしてのみ使用できます。
Microsoft 固有の仕様はここまで