lihao/skynet
1
0
Fork 0
mirror of https://github.com/cloudwu/skynet.git synced 2026-07-22 02:53:09 +00:00
Code Issues Packages Projects Releases Wiki Activity

use _mm_pause (#1433)

Browse Source
This commit is contained in:
colin
2021-07-01 19:29:48 +08:00
committed by GitHub
parent 5c154d34dc
commit 338f53fbe0
1 changed files with 6 additions and 5 deletions
Download Patch File Download Diff File Expand all files Collapse all files

11
skynet-src/spinlock.h
View File

@@ -53,7 +53,8 @@ spinlock_destroy(struct spinlock *lock) {
#define atomic_load_relaxed_(ptr) atomic_load_explicit(ptr, memory_order_relaxed)
#if defined(__x86_64__)
#define atomic_pause_() __builtin_ia32_pause()
#include <immintrin.h> // For _mm_pause
#define atomic_pause_() _mm_pause()
#else
#define atomic_pause_() ((void)0)
#endif
@@ -70,10 +71,10 @@ spinlock_init(struct spinlock *lock) {
static inline void
spinlock_lock(struct spinlock *lock) {
for (;;) {
if (!atomic_test_and_set_(&lock->lock))
return;
while (atomic_load_relaxed_(&lock->lock))
atomic_pause_();
if (!atomic_test_and_set_(&lock->lock))
return;
while (atomic_load_relaxed_(&lock->lock))
atomic_pause_();
}
}