404 Not Found

PATH: lib64 / llvm17 / lib / clang / 17 / include

/*===------------------ uintrintrin.h - UINTR intrinsics -------------------===
 *
 * 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
 *
 *===-----------------------------------------------------------------------===
 */

#ifndef __X86GPRINTRIN_H
#error "Never use <uintrintrin.h> directly; include <x86gprintrin.h> instead."
#endif

#ifndef __UINTRINTRIN_H
#define __UINTRINTRIN_H

/* Define the default attributes for the functions in this file */
#define __DEFAULT_FN_ATTRS \
  __attribute__((__always_inline__, __nodebug__, __target__("uintr")))

#ifdef __x86_64__

struct __uintr_frame
{
  unsigned long long rip;
  unsigned long long rflags;
  unsigned long long rsp;
};

/// Clears the user interrupt flag (UIF). Its effect takes place immediately: a
///    user interrupt cannot be delivered on the instruction boundary following
///    CLUI. Can be executed only if CR4.UINT = 1, the logical processor is in
///    64-bit mode, and software is not executing inside an enclave; otherwise,
///    each causes an invalid-opcode exception. Causes a transactional abort if
///    executed inside a transactional region; the abort loads EAX as it would
///    had it been due to an execution of CLI.
///
/// \headerfile <x86gprintrin.h>
///
/// This intrinsic corresponds to the <c> CLUI </c> instruction.
///
/// \code{.operation}
///   UIF := 0
/// \endcode
static __inline__ void __DEFAULT_FN_ATTRS
_clui (void)
{
  __builtin_ia32_clui();
}

/// Sets the user interrupt flag (UIF). Its effect takes place immediately; a
///    user interrupt may be delivered on the instruction boundary following
///    STUI. Can be executed only if CR4.UINT = 1, the logical processor is in
///    64-bit mode, and software is not executing inside an enclave; otherwise,
///    each causes an invalid-opcode exception. Causes a transactional abort if
///    executed inside a transactional region; the abort loads EAX as it would
///    had it been due to an execution of STI.
///
/// \headerfile <x86gprintrin.h>
///
/// This intrinsic corresponds to the <c> STUI </c> instruction.
///
/// \code{.operation}
///   UIF := 1
/// \endcode
static __inline__ void __DEFAULT_FN_ATTRS
_stui (void)
{
  __builtin_ia32_stui();
}

/// Get the current value of the user interrupt flag (UIF). Can be executed
///    regardless of CPL and inside a transactional region. Can be executed only
///    if CR4.UINT = 1, the logical processor is in 64-bit mode, and software is
///    not executing inside an enclave; otherwise, it causes an invalid-opcode
///    exception.
///
/// \headerfile <x86gprintrin.h>
///
/// This intrinsic corresponds to the <c> TESTUI </c> instruction.
///
/// \returns The current value of the user interrupt flag (UIF).
///
/// \code{.operation}
///   CF := UIF
///   ZF := 0
///   AF := 0
///   OF := 0
///   PF := 0
///   SF := 0
///   dst := CF
/// \endcode
static __inline__ unsigned char __DEFAULT_FN_ATTRS
_testui (void)
{
  return __builtin_ia32_testui();
}

/// Send interprocessor user interrupt. Can be executed only if
///    CR4.UINT = IA32_UINT_TT[0] = 1, the logical processor is in 64-bit mode,
///    and software is not executing inside an enclave; otherwise, it causes an
///    invalid-opcode exception. May be executed at any privilege level, all of
///    its memory accesses are performed with supervisor privilege.
///
/// \headerfile <x86gprintrin.h>
///
/// This intrinsic corresponds to the <c> SENDUIPI </c> instruction
///
/// \param __a
///    Index of user-interrupt target table entry in user-interrupt target
///    table.
///
/// \code{.operation}
///   IF __a > UITTSZ
///     GP (0)
///   FI
///   tempUITTE := MEM[UITTADDR + (a<<4)]
///   // tempUITTE must be valid, and can't have any reserved bit set
///   IF (tempUITTE.V == 0 OR tempUITTE[7:1] != 0)
///     GP (0)
///   FI
///   tempUPID := MEM[tempUITTE.UPIDADDR] // under lock
///   // tempUPID can't have any reserved bit set
///   IF (tempUPID[15:2] != 0 OR tempUPID[31:24] != 0)
///     GP (0) // release lock
///   FI
///   tempUPID.PIR[tempUITTE.UV] := 1;
///   IF (tempUPID.SN == 0 AND tempUPID.ON == 0)
///     tempUPID.ON := 1
///     sendNotify := 1
///   ELSE
///     sendNotify := 0
///   FI
///   MEM[tempUITTE.UPIDADDR] := tempUPID // release lock
///   IF sendNotify == 1
///     IF IA32_APIC_BASE[10] == 1 // local APIC is in x2APIC mode
///       // send ordinary IPI with vector tempUPID.NV to 32-bit physical APIC
///       // ID tempUPID.NDST
///       SendOrdinaryIPI(tempUPID.NV, tempUPID.NDST)
///     ELSE
///       // send ordinary IPI with vector tempUPID.NV to 8-bit physical APIC
///       // ID tempUPID.NDST[15:8]
///       SendOrdinaryIPI(tempUPID.NV, tempUPID.NDST[15:8])
///     FI
///   FI
/// \endcode
static __inline__ void __DEFAULT_FN_ATTRS
_senduipi (unsigned long long __a)
{
  __builtin_ia32_senduipi(__a);
}

#endif /* __x86_64__ */

#undef __DEFAULT_FN_ATTRS

#endif /* __UINTRINTRIN_H */

[+] ..
[-] riscv_ntlh.h [edit]
[-] avx512vlbitalgintrin.h [edit]
[-] avxifmaintrin.h [edit]
[-] mm_malloc.h [edit]
[-] avx512vlbf16intrin.h [edit]
[-] mwaitxintrin.h [edit]
[-] adxintrin.h [edit]
[-] arm_cmse.h [edit]
[-] __clang_cuda_intrinsics.h [edit]
[-] module.modulemap [edit]
[-] crc32intrin.h [edit]
[+] cuda_wrappers
[-] msa.h [edit]
[-] __clang_hip_stdlib.h [edit]
[-] arm_acle.h [edit]
[-] arm_neon_sve_bridge.h [edit]
[-] xsaveintrin.h [edit]
[-] velintrin_gen.h [edit]
[-] stdatomic.h [edit]
[-] hvx_hexagon_protos.h [edit]
[-] uintrintrin.h [edit]
[-] fxsrintrin.h [edit]
[-] sha512intrin.h [edit]
[-] __clang_cuda_texture_intrinsics.h [edit]
[-] iso646.h [edit]
[-] unwind.h [edit]
[-] avx512vlbwintrin.h [edit]
[-] avxvnniint8intrin.h [edit]
[-] avx512erintrin.h [edit]
[-] avxvnniintrin.h [edit]
[-] ia32intrin.h [edit]
[-] rdseedintrin.h [edit]
[-] prfchiintrin.h [edit]
[-] amxcomplexintrin.h [edit]
[-] clflushoptintrin.h [edit]
[-] htmxlintrin.h [edit]
[-] avx512fintrin.h [edit]
[-] gfniintrin.h [edit]
[-] arm_cde.h [edit]
[+] ppc_wrappers
[-] amxfp16intrin.h [edit]
[-] velintrin_approx.h [edit]
[-] avx512pfintrin.h [edit]
[-] stdarg.h [edit]
[-] cmpccxaddintrin.h [edit]
[-] avx512vlintrin.h [edit]
[-] __clang_hip_math.h [edit]
[-] vecintrin.h [edit]
[-] xtestintrin.h [edit]
[-] __wmmintrin_aes.h [edit]
[-] arm_neon.h [edit]
[-] immintrin.h [edit]
[-] ammintrin.h [edit]
[-] waitpkgintrin.h [edit]
[-] vpclmulqdqintrin.h [edit]
[-] fmaintrin.h [edit]
[-] tsxldtrkintrin.h [edit]
[-] prfchwintrin.h [edit]
[-] avx512bitalgintrin.h [edit]
[-] bmiintrin.h [edit]
[-] __wmmintrin_pclmul.h [edit]
[-] htmintrin.h [edit]
[-] mm3dnow.h [edit]
[-] __clang_cuda_builtin_vars.h [edit]
[-] __clang_hip_runtime_wrapper.h [edit]
[-] stdbool.h [edit]
[-] altivec.h [edit]
[-] wbnoinvdintrin.h [edit]
[-] keylockerintrin.h [edit]
[-] tgmath.h [edit]
[-] hexagon_circ_brev_intrinsics.h [edit]
[-] x86intrin.h [edit]
[-] pkuintrin.h [edit]
[-] avx512vbmivlintrin.h [edit]
[-] avxneconvertintrin.h [edit]
[-] __clang_hip_cmath.h [edit]
[-] sgxintrin.h [edit]
[-] f16cintrin.h [edit]
[-] opencl-c-base.h [edit]
[-] cpuid.h [edit]
[-] raointintrin.h [edit]
[-] builtins.h [edit]
[-] emmintrin.h [edit]
[-] smmintrin.h [edit]
[-] vaesintrin.h [edit]
[-] larchintrin.h [edit]
[-] avx512ifmaintrin.h [edit]
[-] intrin.h [edit]
[-] avx512vlvp2intersectintrin.h [edit]
[-] fma4intrin.h [edit]
[-] pmmintrin.h [edit]
[-] __clang_hip_libdevice_declares.h [edit]
[-] limits.h [edit]
[-] clwbintrin.h [edit]
[-] rtmintrin.h [edit]
[-] mmintrin.h [edit]
[-] stddef.h [edit]
[-] invpcidintrin.h [edit]
[-] avx512vp2intersectintrin.h [edit]
[-] cet.h [edit]
[-] xopintrin.h [edit]
[-] avx512vlvnniintrin.h [edit]
[-] avx512vlfp16intrin.h [edit]
[-] stdint.h [edit]
[-] arm64intr.h [edit]
[-] sm4intrin.h [edit]
[-] avx512vnniintrin.h [edit]
[-] avx2intrin.h [edit]
[-] movdirintrin.h [edit]
[-] tbmintrin.h [edit]
[-] arm_mve.h [edit]
[-] avx512ifmavlintrin.h [edit]
[-] amxintrin.h [edit]
[-] opencl-c.h [edit]
[-] stdalign.h [edit]
[-] __clang_cuda_device_functions.h [edit]
[-] pconfigintrin.h [edit]
[-] avx512fp16intrin.h [edit]
[-] inttypes.h [edit]
[-] arm_bf16.h [edit]
[-] __clang_cuda_math_forward_declares.h [edit]
[-] vadefs.h [edit]
[-] shaintrin.h [edit]
[-] hexagon_protos.h [edit]
[-] ptwriteintrin.h [edit]
[-] xsaveoptintrin.h [edit]
[-] enqcmdintrin.h [edit]
[-] x86gprintrin.h [edit]
[-] tmmintrin.h [edit]
[-] stdnoreturn.h [edit]
[-] avx512bf16intrin.h [edit]
[-] varargs.h [edit]
[-] s390intrin.h [edit]
[-] avx512vbmiintrin.h [edit]
[+] openmp_wrappers
[-] wmmintrin.h [edit]
[-] __clang_cuda_cmath.h [edit]
[-] clzerointrin.h [edit]
[-] xsavesintrin.h [edit]
[-] __clang_cuda_libdevice_declares.h [edit]
[-] nmmintrin.h [edit]
[-] wasm_simd128.h [edit]
[-] xsavecintrin.h [edit]
[-] avx512dqintrin.h [edit]
[-] lwpintrin.h [edit]
[-] serializeintrin.h [edit]
[-] arm_sme_draft_spec_subject_to_change.h [edit]
[-] avxintrin.h [edit]
[-] __stddef_max_align_t.h [edit]
[-] sm3intrin.h [edit]
[-] velintrin.h [edit]
[-] __clang_cuda_complex_builtins.h [edit]
[-] armintr.h [edit]
[-] avx512cdintrin.h [edit]
[-] float.h [edit]
[-] avx512vbmi2intrin.h [edit]
[-] lzcntintrin.h [edit]
[-] sifive_vector.h [edit]
[-] rdpruintrin.h [edit]
[-] arm_sve.h [edit]
[-] avx512vpopcntdqintrin.h [edit]
[-] xmmintrin.h [edit]
[-] hresetintrin.h [edit]
[-] bmi2intrin.h [edit]
[-] hexagon_types.h [edit]
[-] avx512bwintrin.h [edit]
[-] cetintrin.h [edit]
[-] __clang_cuda_math.h [edit]
[-] avx512vlvbmi2intrin.h [edit]
[-] arm_fp16.h [edit]
[-] avx512vpopcntdqvlintrin.h [edit]
[-] avxvnniint16intrin.h [edit]
[+] llvm_libc_wrappers
[-] __clang_cuda_runtime_wrapper.h [edit]
[-] cldemoteintrin.h [edit]
[-] avx512vldqintrin.h [edit]
[-] avx512vlcdintrin.h [edit]
[-] popcntintrin.h [edit]