_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	アーキテクチャ	ヘッダー
_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 固有の仕様はここまで

関連項目

コンパイラの組み込み
x86 コンパイラとの競合