1*7330f729Sjoerg /*===---- pkuintrin.h - PKU intrinsics -------------------------------------=== 2*7330f729Sjoerg * 3*7330f729Sjoerg * 4*7330f729Sjoerg * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. 5*7330f729Sjoerg * See https://llvm.org/LICENSE.txt for license information. 6*7330f729Sjoerg * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception 7*7330f729Sjoerg * 8*7330f729Sjoerg *===-----------------------------------------------------------------------=== 9*7330f729Sjoerg */ 10*7330f729Sjoerg #ifndef __IMMINTRIN_H 11*7330f729Sjoerg #error "Never use <pkuintrin.h> directly; include <immintrin.h> instead." 12*7330f729Sjoerg #endif 13*7330f729Sjoerg 14*7330f729Sjoerg #ifndef __PKUINTRIN_H 15*7330f729Sjoerg #define __PKUINTRIN_H 16*7330f729Sjoerg 17*7330f729Sjoerg /* Define the default attributes for the functions in this file. */ 18*7330f729Sjoerg #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("pku"))) 19*7330f729Sjoerg 20*7330f729Sjoerg static __inline__ unsigned int __DEFAULT_FN_ATTRS _rdpkru_u32(void)21*7330f729Sjoerg_rdpkru_u32(void) 22*7330f729Sjoerg { 23*7330f729Sjoerg return __builtin_ia32_rdpkru(); 24*7330f729Sjoerg } 25*7330f729Sjoerg 26*7330f729Sjoerg static __inline__ void __DEFAULT_FN_ATTRS _wrpkru(unsigned int __val)27*7330f729Sjoerg_wrpkru(unsigned int __val) 28*7330f729Sjoerg { 29*7330f729Sjoerg __builtin_ia32_wrpkru(__val); 30*7330f729Sjoerg } 31*7330f729Sjoerg 32*7330f729Sjoerg #undef __DEFAULT_FN_ATTRS 33*7330f729Sjoerg 34*7330f729Sjoerg #endif 35