_InterlockedXor fungsi intrinsik
Khusus Microsoft
Lakukan operasi atom bitwise eksklusif atau (XOR) pada variabel yang dibagikan oleh beberapa utas.
Sintaks
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
);
Parameter
Nilai
[masuk, keluar] Penunjuk ke operand pertama, yang akan digantikan oleh hasilnya.
Masker
[di] Operan kedua.
Nilai hasil
Nilai asli dari operand pertama.
Persyaratan
Intrinsik | Sistem | Header |
---|---|---|
_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> |
Keterangan
Angka dalam nama setiap fungsi menentukan ukuran bit argumen.
Pada platform ARM, gunakan intrinsik dengan _acq
akhiran dan _rel
jika Anda perlu memperoleh dan melepaskan semantik, seperti di awal dan akhir bagian penting. Intrinsik ARM dengan _nf
akhiran ("tanpa pagar") tidak bertindak sebagai pengralang memori.
Intrinsik dengan _np
akhiran ("tidak ada prefetch") mencegah kemungkinan operasi prefetch dimasukkan oleh pengkompilasi.
Pada platform Intel yang mendukung instruksi Hardware Lock Elision (HLE), intrinsik dengan _HLEAcquire
akhiran dan _HLERelease
menyertakan petunjuk ke prosesor yang dapat mempercepat performa dengan menghilangkan langkah tulis kunci di perangkat keras. Jika intrinsik ini dipanggil pada platform yang tidak mendukung HLE, petunjuk diabaikan.
Contoh
// _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
END Khusus Microsoft