From 82ba818ff456bcd6d56a06226e3f27e98fbb55c3 Mon Sep 17 00:00:00 2001 From: Craig Jennings Date: Thu, 14 Aug 2025 22:58:58 -0500 Subject: removing all downloaded devdocs files --- ...memory-model-extensions-for-transactional-memory.html | 16 ---------------- 1 file changed, 16 deletions(-) delete mode 100644 devdocs/gcc~13/x86-specific-memory-model-extensions-for-transactional-memory.html (limited to 'devdocs/gcc~13/x86-specific-memory-model-extensions-for-transactional-memory.html') diff --git a/devdocs/gcc~13/x86-specific-memory-model-extensions-for-transactional-memory.html b/devdocs/gcc~13/x86-specific-memory-model-extensions-for-transactional-memory.html deleted file mode 100644 index daa8ebea..00000000 --- a/devdocs/gcc~13/x86-specific-memory-model-extensions-for-transactional-memory.html +++ /dev/null @@ -1,16 +0,0 @@ -

Next: , Previous: , Up: Extensions to the C Language Family [Contents][Index]

6.57 x86-Specific Memory Model Extensions for Transactional Memory ΒΆ

The x86 architecture supports additional memory ordering flags to mark critical sections for hardware lock elision. These must be specified in addition to an existing memory order to atomic intrinsics.

__ATOMIC_HLE_ACQUIRE

Start lock elision on a lock variable. Memory order must be __ATOMIC_ACQUIRE or stronger.

__ATOMIC_HLE_RELEASE

End lock elision on a lock variable. Memory order must be __ATOMIC_RELEASE or stronger.

When a lock acquire fails, it is required for good performance to abort the transaction quickly. This can be done with a _mm_pause. 

#include <immintrin.h> // For _mm_pause
-
-int lockvar;
-
-/* Acquire lock with lock elision */
-while (__atomic_exchange_n(&lockvar, 1, __ATOMIC_ACQUIRE|__ATOMIC_HLE_ACQUIRE))
-    _mm_pause(); /* Abort failed transaction */
-...
-/* Free lock with lock elision */
-__atomic_store_n(&lockvar, 0, __ATOMIC_RELEASE|__ATOMIC_HLE_RELEASE);
-
-

- © Free Software Foundation
Licensed under the GNU Free Documentation License, Version 1.3.
- https://gcc.gnu.org/onlinedocs/gcc-13.1.0/gcc/x86-specific-memory-model-extensions-for-transactional-memory.html -

-
-- cgit v1.2.3