1*7330f729Sjoerg /*===---- clwbintrin.h - CLWB intrinsic ------------------------------------=== 2*7330f729Sjoerg * 3*7330f729Sjoerg * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. 4*7330f729Sjoerg * See https://llvm.org/LICENSE.txt for license information. 5*7330f729Sjoerg * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception 6*7330f729Sjoerg * 7*7330f729Sjoerg *===-----------------------------------------------------------------------=== 8*7330f729Sjoerg */ 9*7330f729Sjoerg 10*7330f729Sjoerg #ifndef __IMMINTRIN_H 11*7330f729Sjoerg #error "Never use <clwbintrin.h> directly; include <immintrin.h> instead." 12*7330f729Sjoerg #endif 13*7330f729Sjoerg 14*7330f729Sjoerg #ifndef __CLWBINTRIN_H 15*7330f729Sjoerg #define __CLWBINTRIN_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__("clwb"))) 19*7330f729Sjoerg 20*7330f729Sjoerg /// Writes back to memory the cache line (if modified) that contains the 21*7330f729Sjoerg /// linear address specified in \a __p from any level of the cache hierarchy in 22*7330f729Sjoerg /// the cache coherence domain 23*7330f729Sjoerg /// 24*7330f729Sjoerg /// \headerfile <immintrin.h> 25*7330f729Sjoerg /// 26*7330f729Sjoerg /// This intrinsic corresponds to the <c> CLWB </c> instruction. 27*7330f729Sjoerg /// 28*7330f729Sjoerg /// \param __p 29*7330f729Sjoerg /// A pointer to the memory location used to identify the cache line to be 30*7330f729Sjoerg /// written back. 31*7330f729Sjoerg static __inline__ void __DEFAULT_FN_ATTRS _mm_clwb(void const * __p)32*7330f729Sjoerg_mm_clwb(void const *__p) { 33*7330f729Sjoerg __builtin_ia32_clwb(__p); 34*7330f729Sjoerg } 35*7330f729Sjoerg 36*7330f729Sjoerg #undef __DEFAULT_FN_ATTRS 37*7330f729Sjoerg 38*7330f729Sjoerg #endif 39