sync.h

Go to the documentation of this file.

 
#pragma once
 
#include <stdatomic.h>
#include <stdbool.h>
#include <stdint.h>
 
#if defined(__x86_64__) || defined(__i386__)
#include <immintrin.h>
#endif
 
typedef atomic_flag spinlock_t;
 
#define spin_init(lck_p) spin_unlock(lck_p)
 
#if defined(__x86_64__) || defined(__i386__)
#define spin_pause() _mm_pause()
#else
#define spin_pause()
#endif
 
#define spin_lock(lck_p)                                                                                               \
    __extension__({                                                                                                \
        while(atomic_flag_test_and_set_explicit((lck_p), memory_order_acquire))                                \
            spin_pause();                                                                                  \
    })
 
#define spin_trylock(lck_p) !atomic_flag_test_and_set_explicit((lck_p), memory_order_acquire)
 
#define spin_unlock(lck_p) atomic_flag_clear_explicit((lck_p), memory_order_release)
 
extern bool sync_thread_barrier(void);