fonctions intrinsèques _InterlockedAnd

Article
08/04/2024

Section spécifique à Microsoft

Sert à exécuter une opération AND atomique au niveau du bit sur une variable partagée par plusieurs threads.

Syntaxe

long _InterlockedAnd(
   long volatile * value,
   long mask
);
long _InterlockedAnd_acq(
   long volatile * value,
   long mask
);
long _InterlockedAnd_HLEAcquire(
   long volatile * value,
   long mask
);
long _InterlockedAnd_HLERelease(
   long volatile * value,
   long mask
);
long _InterlockedAnd_nf(
   long volatile * value,
   long mask
);
long _InterlockedAnd_np(
   long volatile * value,
   long mask
);
long _InterlockedAnd_rel(
   long volatile * value,
   long mask
);
char _InterlockedAnd8(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_acq(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_nf(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_np(
   char volatile * value,
   char mask
);
char _InterlockedAnd8_rel(
   char volatile * value,
   char mask
);
short _InterlockedAnd16(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_acq(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_nf(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_np(
   short volatile * value,
   short mask
);
short _InterlockedAnd16_rel(
   short volatile * value,
   short mask
);
__int64 _InterlockedAnd64(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_acq(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_HLEAcquire(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_HLERelease(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_nf(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_np(
   __int64 volatile* value,
   __int64 mask
);
__int64 _InterlockedAnd64_rel(
   __int64 volatile* value,
   __int64 mask
);

Paramètres

valeur
[in, out] Pointeur vers le premier opérande, à remplacer par le résultat.

mask
[in] Deuxième opérande.

Valeur retournée

Valeur d’origine du premier opérande.

Spécifications

Intrinsic	Architecture	En-tête
`_InterlockedAnd`, , `_InterlockedAnd8_InterlockedAnd16`	x86, ARM, x64, ARM64	<intrin.h>
`_InterlockedAnd64`	ARM, x64, ARM64	<intrin.h>
`_InterlockedAnd_acq`, , `_InterlockedAnd_nf`, `_InterlockedAnd8_acq`, , `_InterlockedAnd8_rel_InterlockedAnd64_acq_InterlockedAnd64_nf_InterlockedAnd16_acq_InterlockedAnd16_rel_InterlockedAnd16_nf_InterlockedAnd8_nf_InterlockedAnd_rel_InterlockedAnd64_rel`	ARM, ARM64	<intrin.h>
`_InterlockedAnd_np`, , `_InterlockedAnd8_np_InterlockedAnd16_np`, ,`_InterlockedAnd64_np`	x64	<intrin.h>
`_InterlockedAnd_HLEAcquire`, , `_InterlockedAnd_HLERelease_InterlockedAnd64_HLEAcquire`, ,`_InterlockedAnd64_HLERelease`	x86, x64	<immintrin.h>

Notes

Le nombre dans le nom de chaque fonction spécifie la taille en bits des arguments.

Sur les plateformes ARM et ARM64, utilisez les intrinsèques avec _acq et _rel suffixes pour acquérir et libérer la sémantique, comme au début et à la fin d’une section critique. Les fonctions intrinsèques avec un suffixe _nf (pour « no fence », « pas de délimitation ») n'agissent pas comme une barrière mémoire.

Les fonctions intrinsèques avec un suffixe _np (pour « no prefetch », « pas de prérécupération ») empêchent l'insertion par le compilateur d'une possible opération de prérécupération.

Sur les plateformes Intel qui prennent en charge les instructions HLE (Hardware Lock Elision), les fonctions intrinsèques avec les suffixes _HLEAcquire et _HLERelease comprennent une indication pour le processeur qui peut accélérer les performances en éliminant une étape d'écriture de verrou dans le matériel. Si ces fonctions intrinsèques sont appelées sur des plateformes qui ne prennent pas en charge HLE, l'indication est ignorée.

Exemple

// InterlockedAnd.cpp
// Compile with: /Oi
#include <stdio.h>
#include <intrin.h>

#pragma intrinsic(_InterlockedAnd)

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

0xff00 0xffff00 0xff00ff00

FIN de la section spécifique à Microsoft

Voir aussi

Intrinsèques du compilateur
Conflits avec le compilateur x86

Partager via