contrib/llvm-project/clang/lib/Headers/fxsrintrin.h

   1 /*===---- fxsrintrin.h - FXSR 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 <fxsrintrin.h> directly; include <immintrin.h> instead."
  12 #endif
  13
  14 #ifndef __FXSRINTRIN_H
  15 #define __FXSRINTRIN_H
  16
  17 #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__,  __target__("fxsr")))
  18
  19 /// Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte
  20 ///    memory region pointed to by the input parameter \a __p.
  21 ///
  22 /// \headerfile <x86intrin.h>
  23 ///
  24 /// This intrinsic corresponds to the <c> FXSAVE </c> instruction.
  25 ///
  26 /// \param __p
  27 ///    A pointer to a 512-byte memory region. The beginning of this memory
  28 ///    region should be aligned on a 16-byte boundary.
  29 static __inline__ void __DEFAULT_FN_ATTRS
  30 _fxsave(void *__p)
  31 {
  32   __builtin_ia32_fxsave(__p);
  33 }
  34
  35 /// Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte
  36 ///    memory region pointed to by the input parameter \a __p. The contents of
  37 ///    this memory region should have been written to by a previous \c _fxsave
  38 ///    or \c _fxsave64 intrinsic.
  39 ///
  40 /// \headerfile <x86intrin.h>
  41 ///
  42 /// This intrinsic corresponds to the <c> FXRSTOR </c> instruction.
  43 ///
  44 /// \param __p
  45 ///    A pointer to a 512-byte memory region. The beginning of this memory
  46 ///    region should be aligned on a 16-byte boundary.
  47 static __inline__ void __DEFAULT_FN_ATTRS
  48 _fxrstor(void *__p)
  49 {
  50   __builtin_ia32_fxrstor(__p);
  51 }
  52
  53 #ifdef __x86_64__
  54 /// Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte
  55 ///    memory region pointed to by the input parameter \a __p.
  56 ///
  57 /// \headerfile <x86intrin.h>
  58 ///
  59 /// This intrinsic corresponds to the <c> FXSAVE64 </c> instruction.
  60 ///
  61 /// \param __p
  62 ///    A pointer to a 512-byte memory region. The beginning of this memory
  63 ///    region should be aligned on a 16-byte boundary.
  64 static __inline__ void __DEFAULT_FN_ATTRS
  65 _fxsave64(void *__p)
  66 {
  67   __builtin_ia32_fxsave64(__p);
  68 }
  69
  70 /// Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte
  71 ///    memory region pointed to by the input parameter \a __p. The contents of
  72 ///    this memory region should have been written to by a previous \c _fxsave
  73 ///    or \c _fxsave64 intrinsic.
  74 ///
  75 /// \headerfile <x86intrin.h>
  76 ///
  77 /// This intrinsic corresponds to the <c> FXRSTOR64 </c> instruction.
  78 ///
  79 /// \param __p
  80 ///    A pointer to a 512-byte memory region. The beginning of this memory
  81 ///    region should be aligned on a 16-byte boundary.
  82 static __inline__ void __DEFAULT_FN_ATTRS
  83 _fxrstor64(void *__p)
  84 {
  85   __builtin_ia32_fxrstor64(__p);
  86 }
  87 #endif
  88
  89 #undef __DEFAULT_FN_ATTRS
  90
  91 #endif