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