macros.hpp

/**
 * @file
 * @copyright
 *   SPDX-FileCopyrightText: 2022-2024 European Southern Observatory (ESO)
 
 *   SPDX-License-Identifier: LGPL-3.0-only
 */
#ifndef ION_DETAIL_MACROS_HPP
#define ION_DETAIL_MACROS_HPP
 
#include <new>
 
#if defined(__GNUG__)
#include <immintrin.h>  // _mm_pause
#define ION_FORCE_INLINE __attribute__((always_inline))
#define ION_PAUSE(x)     _mm_pause()
#define ION_LIKELY(x)    __builtin_expect(!!(x), 1)
#define ION_UNLIKELY(x)   __builtin_expect(!!(x), 0)
#else
#define ION_FORCE_INLINE
#define ION_PAUSE(x)
#define ION_LIKELY(x)
#define ION_UNLIKELY(x)
#endif
 
#if defined(__SANITIZE_THREAD__)
// tsan does not support memory fences so ion manually annotate those acquire/releases
#include <sanitizer/tsan_interface.h>
#define ION_ANNOTATE_ACQUIRE(x) __tsan_acquire(x)
#define ION_ANNOTATE_RELEASE(x) __tsan_release(x)
#else
#define ION_ANNOTATE_ACQUIRE(x)
#define ION_ANNOTATE_RELEASE(x)
#endif
 
#ifdef __cpp_lib_hardware_interference_size
#define ION_DESTRUCTIVE_INTERFERENCE_SIZE std::hardware_destructive_interference_size
#else
#define ION_DESTRUCTIVE_INTERFERENCE_SIZE 64
#endif
 
#endif  // ION_DETAIL_MACROS_HPP