_InterlockedOr funzioni intrinseche

Articolo
08/04/2024

Sezione specifica Microsoft

Eseguire un'operazione atomica OR bit per bit su una variabile condivisa da più thread.

Sintassi

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
);

Parametri

valore
[in, out] Puntatore al primo operando, da sostituire con il risultato.

Maschera
[in] Secondo operando.

Valore restituito

Valore originale a cui punta il primo parametro.

Requisiti

Intrinsic	Architettura	Intestazione
`_InterlockedOr`, `_InterlockedOr8`, `_InterlockedOr16`	x86, ARM, x64, ARM64	<intrin.h>
`_InterlockedOr64`	ARM, x64, ARM64	<intrin.h>
`_InterlockedOr_acq`, `_InterlockedOr_nf`, , `_InterlockedOr8_acq_InterlockedOr8_nf`, `_InterlockedOr8_rel`, `_InterlockedOr16_acq_InterlockedOr16_rel_InterlockedOr16_nf`, , `_InterlockedOr64_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>

Osservazioni:

Il numero nel nome di ogni funzione specifica la dimensione in bit degli argomenti.

Sulle piattaforme ARM usare le funzioni intrinseche con i suffissi _acq e _rel per la semantica di acquisizione e di rilascio, ad esempio all'inizio e alla fine di una sezione critica. Gli intrinseci ARM con un _nf suffisso ("nessun recinto") non fungono da barriera di memoria.

Le funzioni intrinseche con suffisso _np ("nessuna prelettura") impediscono l'inserimento di una possibile operazione di prelettura da parte del compilatore.

Sulle piattaforme Intel che supportano le istruzioni HLE (Hardware Lock Elision), le funzioni intrinseche con suffissi _HLEAcquire e _HLERelease includono un hint per il processore che consente di accelerare le prestazioni eliminando un passaggio di blocco scrittura nell'hardware. Se queste funzioni intrinseche vengono chiamate su piattaforme che non supportano HLE, l'hint viene ignorato.

Esempio

// _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

Fine sezione specifica Microsoft

Vedi anche

Intrinseci del compilatore
Conflitti con il compilatore x86

Condividi tramite