clang  7.0.0svn
avx512vlbitalgintrin.h
Go to the documentation of this file.
1 /*===------------- avx512vlbitalgintrin.h - BITALG intrinsics ------------------===
2  *
3  *
4  * Permission is hereby granted, free of charge, to any person obtaining a copy
5  * of this software and associated documentation files (the "Software"), to deal
6  * in the Software without restriction, including without limitation the rights
7  * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
8  * copies of the Software, and to permit persons to whom the Software is
9  * furnished to do so, subject to the following conditions:
10  *
11  * The above copyright notice and this permission notice shall be included in
12  * all copies or substantial portions of the Software.
13  *
14  * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
15  * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
16  * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
17  * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
18  * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
19  * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
20  * THE SOFTWARE.
21  *
22  *===-----------------------------------------------------------------------===
23  */
24 #ifndef __IMMINTRIN_H
25 #error "Never use <avx512vlbitalgintrin.h> directly; include <immintrin.h> instead."
26 #endif
27 
28 #ifndef __AVX512VLBITALGINTRIN_H
29 #define __AVX512VLBITALGINTRIN_H
30 
31 /* Define the default attributes for the functions in this file. */
32 #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512vl,avx512bitalg")))
33 
34 static __inline__ __m256i __DEFAULT_FN_ATTRS
35 _mm256_popcnt_epi16(__m256i __A)
36 {
37  return (__m256i) __builtin_ia32_vpopcntw_256((__v16hi) __A);
38 }
39 
40 static __inline__ __m256i __DEFAULT_FN_ATTRS
41 _mm256_mask_popcnt_epi16(__m256i __A, __mmask16 __U, __m256i __B)
42 {
43  return (__m256i) __builtin_ia32_selectw_256((__mmask16) __U,
44  (__v16hi) _mm256_popcnt_epi16(__B),
45  (__v16hi) __A);
46 }
47 
48 static __inline__ __m256i __DEFAULT_FN_ATTRS
50 {
52  __U,
53  __B);
54 }
55 
56 static __inline__ __m128i __DEFAULT_FN_ATTRS
57 _mm128_popcnt_epi16(__m128i __A)
58 {
59  return (__m128i) __builtin_ia32_vpopcntw_128((__v8hi) __A);
60 }
61 
62 static __inline__ __m128i __DEFAULT_FN_ATTRS
63 _mm128_mask_popcnt_epi16(__m128i __A, __mmask8 __U, __m128i __B)
64 {
65  return (__m128i) __builtin_ia32_selectw_128((__mmask8) __U,
66  (__v8hi) _mm128_popcnt_epi16(__B),
67  (__v8hi) __A);
68 }
69 
70 static __inline__ __m128i __DEFAULT_FN_ATTRS
72 {
74  __U,
75  __B);
76 }
77 
78 static __inline__ __m256i __DEFAULT_FN_ATTRS
79 _mm256_popcnt_epi8(__m256i __A)
80 {
81  return (__m256i) __builtin_ia32_vpopcntb_256((__v32qi) __A);
82 }
83 
84 static __inline__ __m256i __DEFAULT_FN_ATTRS
85 _mm256_mask_popcnt_epi8(__m256i __A, __mmask32 __U, __m256i __B)
86 {
87  return (__m256i) __builtin_ia32_selectb_256((__mmask32) __U,
88  (__v32qi) _mm256_popcnt_epi8(__B),
89  (__v32qi) __A);
90 }
91 
92 static __inline__ __m256i __DEFAULT_FN_ATTRS
94 {
96  __U,
97  __B);
98 }
99 
100 static __inline__ __m128i __DEFAULT_FN_ATTRS
101 _mm128_popcnt_epi8(__m128i __A)
102 {
103  return (__m128i) __builtin_ia32_vpopcntb_128((__v16qi) __A);
104 }
105 
106 static __inline__ __m128i __DEFAULT_FN_ATTRS
107 _mm128_mask_popcnt_epi8(__m128i __A, __mmask16 __U, __m128i __B)
108 {
109  return (__m128i) __builtin_ia32_selectb_128((__mmask16) __U,
110  (__v16qi) _mm128_popcnt_epi8(__B),
111  (__v16qi) __A);
112 }
113 
114 static __inline__ __m128i __DEFAULT_FN_ATTRS
116 {
117  return _mm128_mask_popcnt_epi8((__m128i) _mm_setzero_si128(),
118  __U,
119  __B);
120 }
121 
122 static __inline__ __mmask32 __DEFAULT_FN_ATTRS
123 _mm256_mask_bitshuffle_epi32_mask(__mmask32 __U, __m256i __A, __m256i __B)
124 {
125  return (__mmask32) __builtin_ia32_vpshufbitqmb256_mask((__v32qi) __A,
126  (__v32qi) __B,
127  __U);
128 }
129 
130 static __inline__ __mmask32 __DEFAULT_FN_ATTRS
131 _mm256_bitshuffle_epi32_mask(__m256i __A, __m256i __B)
132 {
134  __A,
135  __B);
136 }
137 
138 static __inline__ __mmask16 __DEFAULT_FN_ATTRS
139 _mm128_mask_bitshuffle_epi16_mask(__mmask16 __U, __m128i __A, __m128i __B)
140 {
141  return (__mmask16) __builtin_ia32_vpshufbitqmb128_mask((__v16qi) __A,
142  (__v16qi) __B,
143  __U);
144 }
145 
146 static __inline__ __mmask16 __DEFAULT_FN_ATTRS
147 _mm128_bitshuffle_epi16_mask(__m128i __A, __m128i __B)
148 {
150  __A,
151  __B);
152 }
153 
154 
155 #undef __DEFAULT_FN_ATTRS
156 
157 #endif
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm128_mask_popcnt_epi8(__m128i __A, __mmask16 __U, __m128i __B)
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm256_popcnt_epi8(__m256i __A)
unsigned char __mmask8
Definition: avx512fintrin.h:47
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm128_maskz_popcnt_epi8(__mmask16 __U, __m128i __B)
static __inline__ __mmask16 __DEFAULT_FN_ATTRS _mm128_mask_bitshuffle_epi16_mask(__mmask16 __U, __m128i __A, __m128i __B)
unsigned int __mmask32
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm256_mask_popcnt_epi8(__m256i __A, __mmask32 __U, __m256i __B)
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm256_mask_popcnt_epi16(__m256i __A, __mmask16 __U, __m256i __B)
static __inline__ __mmask32 __DEFAULT_FN_ATTRS _mm256_mask_bitshuffle_epi32_mask(__mmask32 __U, __m256i __A, __m256i __B)
#define __DEFAULT_FN_ATTRS
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm256_popcnt_epi16(__m256i __A)
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm128_mask_popcnt_epi16(__m128i __A, __mmask8 __U, __m128i __B)
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm256_maskz_popcnt_epi8(__mmask32 __U, __m256i __B)
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm128_popcnt_epi8(__m128i __A)
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm128_maskz_popcnt_epi16(__mmask8 __U, __m128i __B)
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm_setzero_si128(void)
Creates a 128-bit integer vector initialized to zero.
Definition: emmintrin.h:3990
static __inline__ __mmask16 __DEFAULT_FN_ATTRS _mm128_bitshuffle_epi16_mask(__m128i __A, __m128i __B)
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm256_maskz_popcnt_epi16(__mmask16 __U, __m256i __B)
static __inline__ __m128i __DEFAULT_FN_ATTRS _mm128_popcnt_epi16(__m128i __A)
static __inline __m256i __DEFAULT_FN_ATTRS _mm256_setzero_si256(void)
Constructs a 256-bit integer vector initialized to zero.
Definition: avxintrin.h:4357
unsigned short __mmask16
Definition: avx512fintrin.h:48
static __inline__ __mmask32 __DEFAULT_FN_ATTRS _mm256_bitshuffle_epi32_mask(__m256i __A, __m256i __B)