次の方法で共有

_InterlockedAnd 組み込み関数

  • [アーティクル]

Microsoft 固有の仕様

複数のスレッドによって共有される変数に対して、ビットごとのアトミックな AND 演算を実行するときに使用します。

構文

long _InterlockedAnd(
   long volatile * value,
   long mask
);
long _InterlockedAnd_acq(
   long volatile * value,
   long mask
);
long _InterlockedAnd_HLEAcquire(
   long volatile * value,
   long mask
);
long _InterlockedAnd_HLERelease(
   long volatile * value,
   long mask
);
long _InterlockedAnd_nf(
   long volatile * value,
   long mask
);
long _InterlockedAnd_np(
   long volatile * value,
   long mask
);
long _InterlockedAnd_rel(
   long volatile * value,
   long mask
);
char _InterlockedAnd8(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_acq(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_nf(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_np(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_rel(
   char volatile * value,
   char mask
);
short _InterlockedAnd16(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_acq(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_nf(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_np(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_rel(
   short volatile * value,
   short mask
);
__int64 _InterlockedAnd64(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_acq(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_HLEAcquire(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_HLERelease(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_nf(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_np(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_rel(
   __int64 volatile* value,
   __int64 mask
);

パラメーター

value
[in, out] 最初のオペランドを指すポインター。結果によって置き換えられます。

マスク‏*
[in] 2 番目のオペランド。

戻り値

最初のオペランドの元の値。

要件

Intrinsic Architecture ヘッダー
_InterlockedAnd、 _InterlockedAnd8、 _InterlockedAnd16 x86、ARM、x64、ARM64 <intrin.h>
_InterlockedAnd64 ARM、x64、ARM64 <intrin.h>
_InterlockedAnd_acq、 _InterlockedAnd_nf、 _InterlockedAnd_rel、 _InterlockedAnd8_acq、 _InterlockedAnd8_nf、 _InterlockedAnd8_rel、 _InterlockedAnd16_acq、 _InterlockedAnd16_nf、 _InterlockedAnd16_rel、 _InterlockedAnd64_acq、 _InterlockedAnd64_nf、 _InterlockedAnd64_rel ARM、ARM64 <intrin.h>
_InterlockedAnd_np、 _InterlockedAnd8_np、 _InterlockedAnd16_np、 _InterlockedAnd64_np x64 <intrin.h>
_InterlockedAnd_HLEAcquire、 _InterlockedAnd_HLERelease、 _InterlockedAnd64_HLEAcquire、 _InterlockedAnd64_HLERelease x86、x64 <immintrin.h>

解説

各関数の名前に含まれる数値は、引数のビット サイズを示しています。

ARM および ARM64 プラットフォームでは、クリティカル セクションの最初と最後などでの取得と解放のセマンティクスのために、_acq および _rel サフィックスの付いた組み込みを使用します。 _nf ("フェンスなし") サフィックスの付いた組み込みはメモリ バリアとしては機能しません。

組み込みに _np ("プリフェッチなし") サフィックスが付いていると、コンパイラによってプリフェッチ操作が挿入される可能性がなくなります。

Hardware Lock Elision (HLE) 命令をサポートする Intel プラットフォームでは、_HLEAcquire および _HLERelease サフィックスの付いた組み込みにプロセッサへのヒントが含まれています。このヒントによりハードウェアでのロック書き込み手順を省くことで、パフォーマンスを向上させることができます。 HLE をサポートしていないプラットフォームでこれらの組み込みが呼び出された場合、ヒントは無視されます。

例

// InterlockedAnd.cpp
// Compile with: /Oi
#include <stdio.h>
#include <intrin.h>

#pragma intrinsic(_InterlockedAnd)

int main()
{
        long data1 = 0xFF00FF00;
        long data2 = 0x00FFFF00;
        long retval;
        retval = _InterlockedAnd(&data1, data2);
        printf_s("0x%x 0x%x 0x%x", data1, data2, retval);
}

0xff00 0xffff00 0xff00ff00

Microsoft 固有の仕様はここまで

関連項目

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