clang/lib/Headers/tsxldtrkintrin.h

   1 /*===------------- tsxldtrkintrin.h - tsxldtrk intrinsics ------------------===
   2  *
   3  * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
   4  * See https://llvm.org/LICENSE.txt for license information.
   5  * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
   6  *
   7  *===-----------------------------------------------------------------------===
   8  */
   9
  10 #ifndef __IMMINTRIN_H
  11 #error "Never use <tsxldtrkintrin.h> directly; include <immintrin.h> instead."
  12 #endif
  13
  14 #ifndef __TSXLDTRKINTRIN_H
  15 #define __TSXLDTRKINTRIN_H
  16
  17 /* Define the default attributes for the functions in this file */
  18 #define _DEFAULT_FN_ATTRS \
  19   __attribute__((__always_inline__, __nodebug__, __target__("tsxldtrk")))
  20
  21 /// Marks the start of an TSX (RTM) suspend load address tracking region. If
  22 ///    this intrinsic is used inside a transactional region, subsequent loads
  23 ///    are not added to the read set of the transaction. If it's used inside a
  24 ///    suspend load address tracking region it will cause transaction abort.
  25 ///    If it's used outside of a transactional region it behaves like a NOP.
  26 ///
  27 /// \headerfile <x86intrin.h>
  28 ///
  29 /// This intrinsic corresponds to the \c XSUSLDTRK instruction.
  30 ///
  31 static __inline__ void _DEFAULT_FN_ATTRS
  32 _xsusldtrk (void)
  33 {
  34     __builtin_ia32_xsusldtrk();
  35 }
  36
  37 /// Marks the end of an TSX (RTM) suspend load address tracking region. If this
  38 ///    intrinsic is used inside a suspend load address tracking region it will
  39 ///    end the suspend region and all following load addresses will be added to
  40 ///    the transaction read set. If it's used inside an active transaction but
  41 ///    not in a suspend region it will cause transaction abort. If it's used
  42 ///    outside of a transactional region it behaves like a NOP.
  43 ///
  44 /// \headerfile <x86intrin.h>
  45 ///
  46 /// This intrinsic corresponds to the \c XRESLDTRK instruction.
  47 ///
  48 static __inline__ void _DEFAULT_FN_ATTRS
  49 _xresldtrk (void)
  50 {
  51     __builtin_ia32_xresldtrk();
  52 }
  53
  54 #undef _DEFAULT_FN_ATTRS
  55
  56 #endif /* __TSXLDTRKINTRIN_H */