次の方法で共有

_InterlockedXor 組み込み関数

  • [アーティクル]

Microsoft 固有の仕様

複数のスレッドによって共有される変数に対して、ビットごとのアトミックな排他的 (XOR) 演算を実行します。

構文

long _InterlockedXor(
   long volatile * Value,
   long Mask
);
long _InterlockedXor_acq(
   long volatile * Value,
   long Mask
);
long _InterlockedXor_HLEAcquire(
   long volatile * Value,
   long Mask
);
long _InterlockedXor_HLERelease(
   long volatile * Value,
   long Mask
);
long _InterlockedXor_nf(
   long volatile * Value,
   long Mask
);
long _InterlockedXor_np(
   long volatile * Value,
   long Mask
);
long _InterlockedXor_rel(
   long volatile * Value,
   long Mask
);
char _InterlockedXor8(
   char volatile * Value,
   char Mask
);
char _InterlockedXor8_acq(
   char volatile * Value,
   char Mask
);
char _InterlockedXor8_nf(
   char volatile * Value,
   char Mask
);
char _InterlockedXor8_np(
   char volatile * Value,
   char Mask
);
char _InterlockedXor8_rel(
   char volatile * Value,
   char Mask
);
short _InterlockedXor16(
   short volatile * Value,
   short Mask
);
short _InterlockedXor16_acq(
   short volatile * Value,
   short Mask
);
short _InterlockedXor16_nf (
   short volatile * Value,
   short Mask
);
short _InterlockedXor16_np (
   short volatile * Value,
   short Mask
);
short _InterlockedXor16_rel(
   short volatile * Value,
   short Mask
);
__int64 _InterlockedXor64(
   __int64 volatile * Value,
   __int64 Mask
);
__int64 _InterlockedXor64_acq(
   __int64 volatile * Value,
   __int64 Mask
);
__int64 _InterlockedXor64_HLEAcquire(
   __int64 volatile * Value,
   __int64 Mask
);
__int64 _InterlockedXor64_HLERelease(
   __int64 volatile * Value,
   __int64 Mask
);
__int64 _InterlockedXor64_nf(
   __int64 volatile * Value,
   __int64 Mask
);
__int64 _InterlockedXor64_np(
   __int64 volatile * Value,
   __int64 Mask
);
__int64 _InterlockedXor64_rel(
   __int64 volatile * Value,
   __int64 Mask
);

パラメーター

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

Mask
[in] 2 番目のオペランド。

戻り値

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

要件

Intrinsic Architecture ヘッダー
_InterlockedXor、 _InterlockedXor8、 _InterlockedXor16 x86、ARM、x64、ARM64 <intrin.h>
_InterlockedXor64 ARM、x64、ARM64 <intrin.h>
_InterlockedXor_acq、 _InterlockedXor_nf、 _InterlockedXor_rel、 _InterlockedXor8_acq、 _InterlockedXor8_nf、 _InterlockedXor8_rel、 _InterlockedXor16_acq、 _InterlockedXor16_nf、 _InterlockedXor16_rel、 _InterlockedXor64_acq、 _InterlockedXor64_nf、 _InterlockedXor64_rel、 ARM、ARM64 <intrin.h>
_InterlockedXor_np、 _InterlockedXor8_np、 _InterlockedXor16_np、 _InterlockedXor64_np X64 <intrin.h>
_InterlockedXor_HLEAcquire, _InterlockedXor_HLERelease x86、x64 <immintrin.h>
_InterlockedXor64_HLEAcquire, _InterlockedXor64_HLERelease X64 <immintrin.h>

解説

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

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

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

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

例

// _InterLockedXor.cpp
#include <stdio.h>
#include <intrin.h>

#pragma intrinsic(_InterlockedXor)

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

0xffff0000 0xffff00 0xff00ff00

Microsoft 固有の仕様はここまで

関連項目

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