#ifndef _IMMINTRIN_H_INCLUDED
#error "Never use <rtmintrin.h> directly; include <immintrin.h> instead."
#endif

#ifndef _RTMINTRIN_H_INCLUDED
#define _RTMINTRIN_H_INCLUDED

#ifndef __RTM__
#pragma GCC push_options
#pragma GCC target("rtm")
#define __DISABLE_RTM__
#endif /* __RTM__ */

#define _XBEGIN_STARTED  (~0u)
#define _XABORT_EXPLICIT (1 << 0)
#define _XABORT_RETRY    (1 << 1)
#define _XABORT_CONFLICT (1 << 2)
#define _XABORT_CAPACITY (1 << 3)
#define _XABORT_DEBUG    (1 << 4)
#define _XABORT_NESTED   (1 << 5)
#define _XABORT_CODE(x)  (((x) >> 24) & 0xFF)

extern __inline unsigned int
    __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    _xbegin(void) {
  return __builtin_ia32_xbegin();
}

extern __inline void
    __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    _xend(void) {
  __builtin_ia32_xend();
}

#ifdef __OPTIMIZE__
extern __inline void
    __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    _xabort(const unsigned int __imm) {
  __builtin_ia32_xabort(__imm);
}
#else
#define _xabort(N) __builtin_ia32_xabort(N)
#endif /* __OPTIMIZE__ */

#ifdef __DISABLE_RTM__
#undef __DISABLE_RTM__
#pragma GCC pop_options
#endif /* __DISABLE_RTM__ */

#endif /* _RTMINTRIN_H_INCLUDED */