85 lines · c
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-exception6 *7 *===-----------------------------------------------------------------------===8 */9 10#ifndef __IMMINTRIN_H11#error "Never use <xsavecintrin.h> directly; include <immintrin.h> instead."12#endif13 14#ifndef __XSAVECINTRIN_H15#define __XSAVECINTRIN_H16 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 at21/// \a __p. The exact state saved depends on the 64-bit mask \a __m and22/// 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 6227/// IF mask[i] == 128/// CASE (i) OF29/// 0: save X87 FPU state30/// 1: save SSE state31/// DEFAULT: __p.Ext_Save_Area[i] := ProcessorState[i]32/// FI33/// ENDFOR34/// __p.Header.XSTATE_BV[62:0] := INIT_FUNCTION(mask[62:0])35/// \endcode36///37/// \headerfile <immintrin.h>38///39/// This intrinsic corresponds to the \c XSAVEC instruction.40///41/// \param __p42/// Pointer to the save area; must be 64-byte aligned.43/// \param __m44/// A 64-bit mask indicating what state should be saved.45static __inline__ void __DEFAULT_FN_ATTRS46_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 at52/// \a __p. The exact state saved depends on the 64-bit mask \a __m and53/// 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 6258/// IF mask[i] == 159/// CASE (i) OF60/// 0: save X87 FPU state61/// 1: save SSE state62/// DEFAULT: __p.Ext_Save_Area[i] := ProcessorState[i]63/// FI64/// ENDFOR65/// __p.Header.XSTATE_BV[62:0] := INIT_FUNCTION(mask[62:0])66/// \endcode67///68/// \headerfile <immintrin.h>69///70/// This intrinsic corresponds to the \c XSAVEC64 instruction.71///72/// \param __p73/// Pointer to the save area; must be 64-byte aligned.74/// \param __m75/// A 64-bit mask indicating what state should be saved.76static __inline__ void __DEFAULT_FN_ATTRS77_xsavec64(void *__p, unsigned long long __m) {78 __builtin_ia32_xsavec64(__p, __m);79}80#endif81 82#undef __DEFAULT_FN_ATTRS83 84#endif85