Warning: This file is not a C or C++ file. It does not have highlighting.
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 \ |
19 | __attribute__((__always_inline__, __nodebug__, \ |
20 | __target__("avx512vbmi,evex512"), __min_vector_width__(512))) |
21 | |
22 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
23 | _mm512_permutex2var_epi8(__m512i __A, __m512i __I, __m512i __B) |
24 | { |
25 | return (__m512i)__builtin_ia32_vpermi2varqi512((__v64qi)__A, (__v64qi)__I, |
26 | (__v64qi) __B); |
27 | } |
28 | |
29 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
30 | _mm512_mask_permutex2var_epi8(__m512i __A, __mmask64 __U, __m512i __I, |
31 | __m512i __B) |
32 | { |
33 | return (__m512i)__builtin_ia32_selectb_512(__U, |
34 | (__v64qi)_mm512_permutex2var_epi8(__A, __I, __B), |
35 | (__v64qi)__A); |
36 | } |
37 | |
38 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
39 | _mm512_mask2_permutex2var_epi8(__m512i __A, __m512i __I, __mmask64 __U, |
40 | __m512i __B) |
41 | { |
42 | return (__m512i)__builtin_ia32_selectb_512(__U, |
43 | (__v64qi)_mm512_permutex2var_epi8(__A, __I, __B), |
44 | (__v64qi)__I); |
45 | } |
46 | |
47 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
48 | _mm512_maskz_permutex2var_epi8(__mmask64 __U, __m512i __A, __m512i __I, |
49 | __m512i __B) |
50 | { |
51 | return (__m512i)__builtin_ia32_selectb_512(__U, |
52 | (__v64qi)_mm512_permutex2var_epi8(__A, __I, __B), |
53 | (__v64qi)_mm512_setzero_si512()); |
54 | } |
55 | |
56 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
57 | _mm512_permutexvar_epi8 (__m512i __A, __m512i __B) |
58 | { |
59 | return (__m512i)__builtin_ia32_permvarqi512((__v64qi) __B, (__v64qi) __A); |
60 | } |
61 | |
62 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
63 | _mm512_maskz_permutexvar_epi8 (__mmask64 __M, __m512i __A, |
64 | __m512i __B) |
65 | { |
66 | return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, |
67 | (__v64qi)_mm512_permutexvar_epi8(__A, __B), |
68 | (__v64qi)_mm512_setzero_si512()); |
69 | } |
70 | |
71 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
72 | _mm512_mask_permutexvar_epi8 (__m512i __W, __mmask64 __M, __m512i __A, |
73 | __m512i __B) |
74 | { |
75 | return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, |
76 | (__v64qi)_mm512_permutexvar_epi8(__A, __B), |
77 | (__v64qi)__W); |
78 | } |
79 | |
80 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
81 | _mm512_multishift_epi64_epi8(__m512i __X, __m512i __Y) |
82 | { |
83 | return (__m512i)__builtin_ia32_vpmultishiftqb512((__v64qi)__X, (__v64qi) __Y); |
84 | } |
85 | |
86 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
87 | _mm512_mask_multishift_epi64_epi8(__m512i __W, __mmask64 __M, __m512i __X, |
88 | __m512i __Y) |
89 | { |
90 | return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, |
91 | (__v64qi)_mm512_multishift_epi64_epi8(__X, __Y), |
92 | (__v64qi)__W); |
93 | } |
94 | |
95 | static __inline__ __m512i __DEFAULT_FN_ATTRS |
96 | _mm512_maskz_multishift_epi64_epi8(__mmask64 __M, __m512i __X, __m512i __Y) |
97 | { |
98 | return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M, |
99 | (__v64qi)_mm512_multishift_epi64_epi8(__X, __Y), |
100 | (__v64qi)_mm512_setzero_si512()); |
101 | } |
102 | |
103 | |
104 | #undef __DEFAULT_FN_ATTRS |
105 | |
106 | #endif |
107 |
Warning: This file is not a C or C++ file. It does not have highlighting.