1*0b57cec5SDimitry Andric /*===---- xtestintrin.h - XTEST intrinsic ----------------------------------=== 2*0b57cec5SDimitry Andric * 3*0b57cec5SDimitry Andric * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. 4*0b57cec5SDimitry Andric * See https://llvm.org/LICENSE.txt for license information. 5*0b57cec5SDimitry Andric * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception 6*0b57cec5SDimitry Andric * 7*0b57cec5SDimitry Andric *===-----------------------------------------------------------------------=== 8*0b57cec5SDimitry Andric */ 9*0b57cec5SDimitry Andric 10*0b57cec5SDimitry Andric #ifndef __IMMINTRIN_H 11*0b57cec5SDimitry Andric #error "Never use <xtestintrin.h> directly; include <immintrin.h> instead." 12*0b57cec5SDimitry Andric #endif 13*0b57cec5SDimitry Andric 14*0b57cec5SDimitry Andric #ifndef __XTESTINTRIN_H 15*0b57cec5SDimitry Andric #define __XTESTINTRIN_H 16*0b57cec5SDimitry Andric 17*0b57cec5SDimitry Andric /* xtest returns non-zero if the instruction is executed within an RTM or active 18*0b57cec5SDimitry Andric * HLE region. */ 19*0b57cec5SDimitry Andric /* FIXME: This can be an either or for RTM/HLE. Deal with this when HLE is 20*0b57cec5SDimitry Andric * supported. */ 21*0b57cec5SDimitry Andric static __inline__ int 22*0b57cec5SDimitry Andric __attribute__((__always_inline__, __nodebug__, __target__("rtm"))) _xtest(void)23*0b57cec5SDimitry Andric _xtest(void) { 24*0b57cec5SDimitry Andric return __builtin_ia32_xtest(); 25*0b57cec5SDimitry Andric } 26*0b57cec5SDimitry Andric 27*0b57cec5SDimitry Andric #endif 28