funkcje wewnętrzne _InterlockedXor
Specyficzne dla firmy Microsoft
Wykonaj niepodzielne operacje wykluczające bitowe lub (XOR) na zmiennej współużytkowanej przez wiele wątków.
Składnia
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
);
Parametry
Wartość
[in, out] Wskaźnik do pierwszego operandu, który ma zostać zastąpiony przez wynik.
Maska
[in] Drugi operand.
Wartość zwracana
Oryginalna wartość pierwszego operandu.
Wymagania
| Nieodłączny | Architektura | Nagłówek |
|---|---|---|
_InterlockedXor, , _InterlockedXor8_InterlockedXor16 |
x86, ARM, x64, ARM64 | <intrin.h> |
_InterlockedXor64 |
ARM, x64, ARM64 | <intrin.h> |
_InterlockedXor_acq, _InterlockedXor_nf, , , _InterlockedXor8_nf_InterlockedXor16_nf_InterlockedXor8_acq_InterlockedXor16_acq_InterlockedXor64_rel_InterlockedXor8_rel_InterlockedXor16_rel_InterlockedXor64_acq_InterlockedXor64_nf_InterlockedXor_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> |
Uwagi
Liczba w nazwie każdej funkcji określa rozmiar bitów argumentów.
Na platformach ARM użyj funkcji wewnętrznych i _acq _rel sufiksów, jeśli potrzebujesz semantyki uzyskiwania i wydawania, takich jak na początku i na końcu sekcji krytycznej. Funkcje wewnętrzne arm z sufiksem _nf ("bez ogrodzenia") nie działają jako bariera pamięci.
Funkcje wewnętrzne z sufiksem _np ("brak pobierania wstępnego") uniemożliwiają wstawienie możliwej operacji pobierania wstępnego przez kompilator.
Na platformach Intel, które obsługują instrukcje dotyczące blokady sprzętu Elision (HLE), funkcje wewnętrzne z sufiksami _HLEAcquire zawierają _HLERelease wskazówkę dla procesora, który może przyspieszyć wydajność, eliminując krok zapisu blokady w sprzęcie. Jeśli te funkcje wewnętrzne są wywoływane na platformach, które nie obsługują HLE, wskazówka jest ignorowana.
Przykład
// _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 Microsoft Specific