funkcje wewnętrzne _InterlockedOr
Specyficzne dla firmy Microsoft
Wykonaj niepodzielne bitowe lub operację na zmiennej współużytkowanej przez wiele wątków.
Składnia
long _InterlockedOr(
long volatile * Value,
long Mask
);
long _InterlockedOr_acq(
long volatile * Value,
long Mask
);
long _InterlockedOr_HLEAcquire(
long volatile * Value,
long Mask
);
long _InterlockedOr_HLERelease(
long volatile * Value,
long Mask
);
long _InterlockedOr_nf(
long volatile * Value,
long Mask
);
long _InterlockedOr_np(
long volatile * Value,
long Mask
);
long _InterlockedOr_rel(
long volatile * Value,
long Mask
);
char _InterlockedOr8(
char volatile * Value,
char Mask
);
char _InterlockedOr8_acq(
char volatile * Value,
char Mask
);
char _InterlockedOr8_nf(
char volatile * Value,
char Mask
);
char _InterlockedOr8_np(
char volatile * Value,
char Mask
);
char _InterlockedOr8_rel(
char volatile * Value,
char Mask
);
short _InterlockedOr16(
short volatile * Value,
short Mask
);
short _InterlockedOr16_acq(
short volatile * Value,
short Mask
);
short _InterlockedOr16_nf(
short volatile * Value,
short Mask
);
short _InterlockedOr16_np(
short volatile * Value,
short Mask
);
short _InterlockedOr16_rel(
short volatile * Value,
short Mask
);
__int64 _InterlockedOr64(
__int64 volatile * Value,
__int64 Mask
);
__int64 _InterlockedOr64_acq(
__int64 volatile * Value,
__int64 Mask
);
__int64 _InterlockedOr64_HLEAcquire(
__int64 volatile * Value,
__int64 Mask
);
__int64 _InterlockedOr64_HLERelease(
__int64 volatile * Value,
__int64 Mask
);
__int64 _InterlockedOr64_nf(
__int64 volatile * Value,
__int64 Mask
);
__int64 _InterlockedOr64_np(
__int64 volatile * Value,
__int64 Mask
);
__int64 _InterlockedOr64_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ść wskazywana przez pierwszy parametr.
Wymagania
| Nieodłączny | Architektura | Nagłówek |
|---|---|---|
_InterlockedOr, , _InterlockedOr8_InterlockedOr16 |
x86, ARM, x64, ARM64 | <intrin.h> |
_InterlockedOr64 |
ARM, x64, ARM64 | <intrin.h> |
_InterlockedOr_acq, _InterlockedOr_nf, , , _InterlockedOr8_nf_InterlockedOr16_rel_InterlockedOr8_rel_InterlockedOr64_nf_InterlockedOr8_acq_InterlockedOr16_acq_InterlockedOr16_nf_InterlockedOr64_acq_InterlockedOr_rel_InterlockedOr64_rel |
ARM, ARM64 | <intrin.h> |
_InterlockedOr_np, , _InterlockedOr8_np, , _InterlockedOr16_np_InterlockedOr64_np |
x64 | <intrin.h> |
_InterlockedOr_HLEAcquire, _InterlockedOr_HLERelease |
x86, x64 | <immintrin.h> |
_InterlockedOr64_HLEAcquire, _InterlockedOr64_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
// _InterlockedOr.cpp
#include <stdio.h>
#include <intrin.h>
#pragma intrinsic(_InterlockedOr)
int main()
{
long data1 = 0xFF00FF00;
long data2 = 0x00FFFF00;
long retval;
retval = _InterlockedOr(&data1, data2);
printf_s("0x%x 0x%x 0x%x", data1, data2, retval);
}
0xffffff00 0xffff00 0xff00ff00
END Microsoft Specific