1*67e74705SXin Li /*===---- xtestintrin.h - XTEST intrinsic ---------------------------------=== 2*67e74705SXin Li * 3*67e74705SXin Li * Permission is hereby granted, free of charge, to any person obtaining a copy 4*67e74705SXin Li * of this software and associated documentation files (the "Software"), to deal 5*67e74705SXin Li * in the Software without restriction, including without limitation the rights 6*67e74705SXin Li * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell 7*67e74705SXin Li * copies of the Software, and to permit persons to whom the Software is 8*67e74705SXin Li * furnished to do so, subject to the following conditions: 9*67e74705SXin Li * 10*67e74705SXin Li * The above copyright notice and this permission notice shall be included in 11*67e74705SXin Li * all copies or substantial portions of the Software. 12*67e74705SXin Li * 13*67e74705SXin Li * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR 14*67e74705SXin Li * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY, 15*67e74705SXin Li * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE 16*67e74705SXin Li * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER 17*67e74705SXin Li * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM, 18*67e74705SXin Li * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN 19*67e74705SXin Li * THE SOFTWARE. 20*67e74705SXin Li * 21*67e74705SXin Li *===-----------------------------------------------------------------------=== 22*67e74705SXin Li */ 23*67e74705SXin Li 24*67e74705SXin Li #ifndef __IMMINTRIN_H 25*67e74705SXin Li #error "Never use <xtestintrin.h> directly; include <immintrin.h> instead." 26*67e74705SXin Li #endif 27*67e74705SXin Li 28*67e74705SXin Li #ifndef __XTESTINTRIN_H 29*67e74705SXin Li #define __XTESTINTRIN_H 30*67e74705SXin Li 31*67e74705SXin Li /* xtest returns non-zero if the instruction is executed within an RTM or active 32*67e74705SXin Li * HLE region. */ 33*67e74705SXin Li /* FIXME: This can be an either or for RTM/HLE. Deal with this when HLE is 34*67e74705SXin Li * supported. */ 35*67e74705SXin Li static __inline__ int 36*67e74705SXin Li __attribute__((__always_inline__, __nodebug__, __target__("rtm"))) _xtest(void)37*67e74705SXin Li _xtest(void) { 38*67e74705SXin Li return __builtin_ia32_xtest(); 39*67e74705SXin Li } 40*67e74705SXin Li 41*67e74705SXin Li #endif 42