1*0b57cec5SDimitry Andric /*===---- clwbintrin.h - CLWB 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 <clwbintrin.h> directly; include <immintrin.h> instead." 12*0b57cec5SDimitry Andric #endif 13*0b57cec5SDimitry Andric 14*0b57cec5SDimitry Andric #ifndef __CLWBINTRIN_H 15*0b57cec5SDimitry Andric #define __CLWBINTRIN_H 16*0b57cec5SDimitry Andric 17*0b57cec5SDimitry Andric /* Define the default attributes for the functions in this file. */ 18*0b57cec5SDimitry Andric #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("clwb"))) 19*0b57cec5SDimitry Andric 20*0b57cec5SDimitry Andric /// Writes back to memory the cache line (if modified) that contains the 21*0b57cec5SDimitry Andric /// linear address specified in \a __p from any level of the cache hierarchy in 22*0b57cec5SDimitry Andric /// the cache coherence domain 23*0b57cec5SDimitry Andric /// 24*0b57cec5SDimitry Andric /// \headerfile <immintrin.h> 25*0b57cec5SDimitry Andric /// 26*0b57cec5SDimitry Andric /// This intrinsic corresponds to the <c> CLWB </c> instruction. 27*0b57cec5SDimitry Andric /// 28*0b57cec5SDimitry Andric /// \param __p 29*0b57cec5SDimitry Andric /// A pointer to the memory location used to identify the cache line to be 30*0b57cec5SDimitry Andric /// written back. 31*0b57cec5SDimitry Andric static __inline__ void __DEFAULT_FN_ATTRS _mm_clwb(void const * __p)32*0b57cec5SDimitry Andric_mm_clwb(void const *__p) { 33*0b57cec5SDimitry Andric __builtin_ia32_clwb(__p); 34*0b57cec5SDimitry Andric } 35*0b57cec5SDimitry Andric 36*0b57cec5SDimitry Andric #undef __DEFAULT_FN_ATTRS 37*0b57cec5SDimitry Andric 38*0b57cec5SDimitry Andric #endif 39