clang/lib/Headers/xsavecintrin.h

   1 /*===---- xsavecintrin.h - XSAVEC intrinsic --------------------------------===
   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 <xsavecintrin.h> directly; include <immintrin.h> instead."
  12 #endif
  13
  14 #ifndef __XSAVECINTRIN_H
  15 #define __XSAVECINTRIN_H
  16
  17 /* Define the default attributes for the functions in this file. */
  18 #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__,  __target__("xsavec")))
  19
  20 /// Performs a full or partial save of processor state to the memory at
  21 ///    \a __p. The exact state saved depends on the 64-bit mask \a __m and
  22 ///    processor control register \c XCR0.
  23 ///
  24 /// \code{.operation}
  25 /// mask[62:0] := __m[62:0] AND XCR0[62:0]
  26 /// FOR i := 0 TO 62
  27 ///   IF mask[i] == 1
  28 ///     CASE (i) OF
  29 ///     0: save X87 FPU state
  30 ///     1: save SSE state
  31 ///     DEFAULT: __p.Ext_Save_Area[i] := ProcessorState[i]
  32 ///   FI
  33 /// ENDFOR
  34 /// __p.Header.XSTATE_BV[62:0] := INIT_FUNCTION(mask[62:0])
  35 /// \endcode
  36 ///
  37 /// \headerfile <immintrin.h>
  38 ///
  39 /// This intrinsic corresponds to the \c XSAVEC instruction.
  40 ///
  41 /// \param __p
  42 ///    Pointer to the save area; must be 64-byte aligned.
  43 /// \param __m
  44 ///    A 64-bit mask indicating what state should be saved.
  45 static __inline__ void __DEFAULT_FN_ATTRS
  46 _xsavec(void *__p, unsigned long long __m) {
  47   __builtin_ia32_xsavec(__p, __m);
  48 }
  49
  50 #ifdef __x86_64__
  51 /// Performs a full or partial save of processor state to the memory at
  52 ///    \a __p. The exact state saved depends on the 64-bit mask \a __m and
  53 ///    processor control register \c XCR0.
  54 ///
  55 /// \code{.operation}
  56 /// mask[62:0] := __m[62:0] AND XCR0[62:0]
  57 /// FOR i := 0 TO 62
  58 ///   IF mask[i] == 1
  59 ///     CASE (i) OF
  60 ///     0: save X87 FPU state
  61 ///     1: save SSE state
  62 ///     DEFAULT: __p.Ext_Save_Area[i] := ProcessorState[i]
  63 ///   FI
  64 /// ENDFOR
  65 /// __p.Header.XSTATE_BV[62:0] := INIT_FUNCTION(mask[62:0])
  66 /// \endcode
  67 ///
  68 /// \headerfile <immintrin.h>
  69 ///
  70 /// This intrinsic corresponds to the \c XSAVEC64 instruction.
  71 ///
  72 /// \param __p
  73 ///    Pointer to the save area; must be 64-byte aligned.
  74 /// \param __m
  75 ///    A 64-bit mask indicating what state should be saved.
  76 static __inline__ void __DEFAULT_FN_ATTRS
  77 _xsavec64(void *__p, unsigned long long __m) {
  78   __builtin_ia32_xsavec64(__p, __m);
  79 }
  80 #endif
  81
  82 #undef __DEFAULT_FN_ATTRS
  83
  84 #endif