1/*===------------- avx512vbmiintrin.h - VBMI intrinsics ------------------=== 2 * 3 * 4 * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. 5 * See https://llvm.org/LICENSE.txt for license information. 6 * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception 7 * 8 *===-----------------------------------------------------------------------=== 9 */ 10#ifndef __IMMINTRIN_H 11#error "Never use <avx512vbmiintrin.h> directly; include <immintrin.h> instead." 12#endif 13 14#ifndef __VBMIINTRIN_H 15#define __VBMIINTRIN_H 16 17/* Define the default attributes for the functions in this file. */ 18#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512vbmi"), __min_vector_width__(512))) 19 20 21static __inline__ __m512i __DEFAULT_FN_ATTRS 22_mm512_permutex2var_epi8(__m512i __A, __m512i __I, __m512i __B) 23{ 24 return (__m512i)__builtin_ia32_vpermi2varqi512((__v64qi)__A, (__v64qi)__I, 25 (__v64qi) __B); 26} 27 28static __inline__ __m512i __DEFAULT_FN_ATTRS 29_mm512_mask_permutex2var_epi8(__m512i __A, __mmask64 __U, __m512i __I, 30 __m512i __B) 31{ 32 return (__m512i)__builtin_ia32_selectb_512(__U, 33 (__v64qi)_mm512_permutex2var_epi8(__A, __I, __B), 34 (__v64qi)__A); 35} 36 37static __inline__ __m512i __DEFAULT_FN_ATTRS 38_mm512_mask2_permutex2var_epi8(__m512i __A, __m512i __I, __mmask64 __U, 39 __m512i __B) 40{ 41 return (__m512i)__builtin_ia32_selectb_512(__U, 42 (__v64qi)_mm512_permutex2var_epi8(__A, __I, __B), 43 (__v64qi)__I); 44} 45 46static __inline__ __m512i __DEFAULT_FN_ATTRS 47_mm512_maskz_permutex2var_epi8(__mmask64 __U, __m512i __A, __m512i __I, 48 __m512i __B) 49{ 50 return (__m512i)__builtin_ia32_selectb_512(__U, 51 (__v64qi)_mm512_permutex2var_epi8(__A, __I, __B), 52 (__v64qi)_mm512_setzero_si512()); 53} 54 55static __inline__ __m512i __DEFAULT_FN_ATTRS 56_mm512_permutexvar_epi8 (__m512i __A, __m512i __B) 57{ 58 return (__m512i)__builtin_ia32_permvarqi512((__v64qi) __B, (__v64qi) __A); 59} 60 61static __inline__ __m512i __DEFAULT_FN_ATTRS 62_mm512_maskz_permutexvar_epi8 (__mmask64 __M, __m512i __A, 63 __m512i __B) 64{ 65 return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, 66 (__v64qi)_mm512_permutexvar_epi8(__A, __B), 67 (__v64qi)_mm512_setzero_si512()); 68} 69 70static __inline__ __m512i __DEFAULT_FN_ATTRS 71_mm512_mask_permutexvar_epi8 (__m512i __W, __mmask64 __M, __m512i __A, 72 __m512i __B) 73{ 74 return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, 75 (__v64qi)_mm512_permutexvar_epi8(__A, __B), 76 (__v64qi)__W); 77} 78 79static __inline__ __m512i __DEFAULT_FN_ATTRS 80_mm512_multishift_epi64_epi8(__m512i __X, __m512i __Y) 81{ 82 return (__m512i)__builtin_ia32_vpmultishiftqb512((__v64qi)__X, (__v64qi) __Y); 83} 84 85static __inline__ __m512i __DEFAULT_FN_ATTRS 86_mm512_mask_multishift_epi64_epi8(__m512i __W, __mmask64 __M, __m512i __X, 87 __m512i __Y) 88{ 89 return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, 90 (__v64qi)_mm512_multishift_epi64_epi8(__X, __Y), 91 (__v64qi)__W); 92} 93 94static __inline__ __m512i __DEFAULT_FN_ATTRS 95_mm512_maskz_multishift_epi64_epi8(__mmask64 __M, __m512i __X, __m512i __Y) 96{ 97 return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, 98 (__v64qi)_mm512_multishift_epi64_epi8(__X, __Y), 99 (__v64qi)_mm512_setzero_si512()); 100} 101 102 103#undef __DEFAULT_FN_ATTRS 104 105#endif 106