встроенные функции _InterlockedExchange

Статья
08/04/2024

Блок, относящийся только к системам Майкрософт

Создает атомарные инструкция для присваивания заданного значения.

Синтаксис

long _InterlockedExchange(
   long volatile * Target,
   long Value
);
long _InterlockedExchange_acq(
   long volatile * Target,
   long Value
);
long _InterlockedExchange_HLEAcquire(
   long volatile * Target,
   long Value
);
long _InterlockedExchange_HLERelease(
   long volatile * Target,
   long Value
);
long _InterlockedExchange_nf(
   long volatile * Target,
   long Value
);
long _InterlockedExchange_rel(
   long volatile * Target,
   long Value
);
char _InterlockedExchange8(
   char volatile * Target,
   char Value
);
char _InterlockedExchange8_acq(
   char volatile * Target,
   char Value
);
char _InterlockedExchange8_nf(
   char volatile * Target,
   char Value
);
char _InterlockedExchange8_rel(
   char volatile * Target,
   char Value
);
short _InterlockedExchange16(
   short volatile * Target,
   short Value
);
short _InterlockedExchange16_acq(
   short volatile * Target,
   short Value
);
short _InterlockedExchange16_nf(
   short volatile * Target,
   short Value
);
short _InterlockedExchange16_rel(
   short volatile * Target,
   short Value
);
__int64 _InterlockedExchange64(
   __int64 volatile * Target,
   __int64 Value
);
__int64 _InterlockedExchange64_acq(
   __int64 volatile * Target,
   __int64 Value
);
__int64 _InterlockedExchange64_HLEAcquire(
   __int64 volatile * Target,
   __int64 Value
);
__int64 _InterlockedExchange64_HLERelease(
   __int64 volatile * Target,
   __int64 Value
);
__int64 _InterlockedExchange64_nf(
   __int64 volatile * Target,
   __int64 Value
);
__int64 _InterlockedExchange64_rel(
   __int64 volatile * Target,
   __int64 Value
);

Параметры

Целевой объект
[in, out] Указатель на значение для обмена. Функция присваивает этой переменной Value и возвращает предыдущее значение.

Value
[in] Значение для обмена значением Target, на которое указывает значение.

Возвращаемое значение

Возвращает начальное значение, на которое указывает Target.

Требования

Intrinsic	Архитектура	Верхний колонтитул
`_InterlockedExchange`, , `_InterlockedExchange8_InterlockedExchange16`	x86, ARM, x64, ARM64	<intrin.h>
`_InterlockedExchange64`	ARM, x64, ARM64	<intrin.h>
`_InterlockedExchange_acq`, `_InterlockedExchange_nf`, `_InterlockedExchange_rel_InterlockedExchange8_acq_InterlockedExchange8_nf_InterlockedExchange8_rel_InterlockedExchange16_acq_InterlockedExchange16_nf_InterlockedExchange16_rel_InterlockedExchange64_acq_InterlockedExchange64_nf_InterlockedExchange64_rel`	ARM, ARM64	<intrin.h>
`_InterlockedExchange_HLEAcquire`, `_InterlockedExchange_HLERelease`	x86, x64	<immintrin.h>
`_InterlockedExchange64_HLEAcquire`, `_InterlockedExchange64_HLERelease`	x64	<immintrin.h>

Замечания

_InterlockedExchangeпредоставляет встроенную поддержку компилятора для функции InterlockedExchange пакета SDK для Win32 Windows.

Существуют несколько вариантов _InterlockedExchange, они различаются в зависимости от типов данных, которые включают, и от того, используется ли семантика получения или освобождения конкретного процессора.

Функция _InterlockedExchange работает с 32-разрядными целыми значениями, _InterlockedExchange8работает с 8-разрядными целыми значениями, _InterlockedExchange16 работает с 16-разрядными целыми значениями и _InterlockedExchange64 работает с 64-разрядными целыми значениями.

На платформах ARM используются встроенные функции с суффиксами _acq и _rel для получения и освобождения семантики, например, в начале и конце критической секции. Встроенные компоненты с суффиксом _nf ("без забора") не действуют в качестве барьера памяти.

На платформах Intel ®, поддерживающих инструкции Hardware Lock Elision (HLE), встроенные функции с суффиксами _HLEAcquire и _HLERelease включают подсказку процессору, как можно повысить производительность, устраняя шаг записи с блокировкой оборудования. Если эти встроенные функции вызываются на платформах, не поддерживающих HLE, подсказка игнорируется.

Эти процедуры доступны только как встроенные объекты.

Пример

Пример использования _InterlockedExchangeсм. в _InterlockedDecrement.

Завершение блока, относящегося только к системам Майкрософт

См. также

Встроенные компоненты компилятора
Ключевые слова
Конфликты с 32-разрядным (x86) компилятором

Поделиться через