zig/lib/include/fxsrintrin.h

92 lines
2.8 KiB
C
Raw Normal View History

2015-12-08 16:51:59 -08:00
/*===---- fxsrintrin.h - FXSR intrinsic ------------------------------------===
*
* Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
* See https://llvm.org/LICENSE.txt for license information.
* SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
2015-12-08 16:51:59 -08:00
*
*===-----------------------------------------------------------------------===
*/
#ifndef __IMMINTRIN_H
#error "Never use <fxsrintrin.h> directly; include <immintrin.h> instead."
#endif
#ifndef __FXSRINTRIN_H
#define __FXSRINTRIN_H
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("fxsr")))
2015-12-08 16:51:59 -08:00
2018-08-04 23:20:05 -07:00
/// Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte
/// memory region pointed to by the input parameter \a __p.
///
/// \headerfile <x86intrin.h>
///
/// This intrinsic corresponds to the <c> FXSAVE </c> instruction.
///
/// \param __p
/// A pointer to a 512-byte memory region. The beginning of this memory
/// region should be aligned on a 16-byte boundary.
2015-12-08 16:51:59 -08:00
static __inline__ void __DEFAULT_FN_ATTRS
_fxsave(void *__p)
{
2018-08-04 23:20:05 -07:00
__builtin_ia32_fxsave(__p);
2015-12-08 16:51:59 -08:00
}
2018-08-04 23:20:05 -07:00
/// Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte
/// memory region pointed to by the input parameter \a __p. The contents of
/// this memory region should have been written to by a previous \c _fxsave
/// or \c _fxsave64 intrinsic.
///
/// \headerfile <x86intrin.h>
///
/// This intrinsic corresponds to the <c> FXRSTOR </c> instruction.
///
/// \param __p
/// A pointer to a 512-byte memory region. The beginning of this memory
/// region should be aligned on a 16-byte boundary.
2015-12-08 16:51:59 -08:00
static __inline__ void __DEFAULT_FN_ATTRS
_fxrstor(void *__p)
{
2018-08-04 23:20:05 -07:00
__builtin_ia32_fxrstor(__p);
2015-12-08 16:51:59 -08:00
}
#ifdef __x86_64__
2018-08-04 23:20:05 -07:00
/// Saves the XMM, MMX, MXCSR and x87 FPU registers into a 512-byte
/// memory region pointed to by the input parameter \a __p.
///
/// \headerfile <x86intrin.h>
///
/// This intrinsic corresponds to the <c> FXSAVE64 </c> instruction.
///
/// \param __p
/// A pointer to a 512-byte memory region. The beginning of this memory
/// region should be aligned on a 16-byte boundary.
2015-12-08 16:51:59 -08:00
static __inline__ void __DEFAULT_FN_ATTRS
_fxsave64(void *__p)
{
2018-08-04 23:20:05 -07:00
__builtin_ia32_fxsave64(__p);
2015-12-08 16:51:59 -08:00
}
2018-08-04 23:20:05 -07:00
/// Restores the XMM, MMX, MXCSR and x87 FPU registers from the 512-byte
/// memory region pointed to by the input parameter \a __p. The contents of
/// this memory region should have been written to by a previous \c _fxsave
/// or \c _fxsave64 intrinsic.
///
/// \headerfile <x86intrin.h>
///
/// This intrinsic corresponds to the <c> FXRSTOR64 </c> instruction.
///
/// \param __p
/// A pointer to a 512-byte memory region. The beginning of this memory
/// region should be aligned on a 16-byte boundary.
2015-12-08 16:51:59 -08:00
static __inline__ void __DEFAULT_FN_ATTRS
_fxrstor64(void *__p)
{
2018-08-04 23:20:05 -07:00
__builtin_ia32_fxrstor64(__p);
2015-12-08 16:51:59 -08:00
}
#endif
2015-12-08 16:51:59 -08:00
#undef __DEFAULT_FN_ATTRS
#endif