contrib/llvm/tools/clang/lib/Headers/avx512vpopcntdqintrin.h

   1 /*===----- avx512vpopcntdqintrin.h - AVX512VPOPCNTDQ 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                                                                         \
  26     "Never use <avx512vpopcntdqintrin.h> directly; include <immintrin.h> instead."
  27 #endif
  28
  29 #ifndef __AVX512VPOPCNTDQINTRIN_H
  30 #define __AVX512VPOPCNTDQINTRIN_H
  31
  32 /* Define the default attributes for the functions in this file. */
  33 #define __DEFAULT_FN_ATTRS                                                     \
  34   __attribute__((__always_inline__, __nodebug__, __target__("avx512vpopcntdq"), __min_vector_width__(512)))
  35
  36 static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_popcnt_epi64(__m512i __A) {
  37   return (__m512i)__builtin_ia32_vpopcntq_512((__v8di)__A);
  38 }
  39
  40 static __inline__ __m512i __DEFAULT_FN_ATTRS
  41 _mm512_mask_popcnt_epi64(__m512i __W, __mmask8 __U, __m512i __A) {
  42   return (__m512i)__builtin_ia32_selectq_512(
  43       (__mmask8)__U, (__v8di)_mm512_popcnt_epi64(__A), (__v8di)__W);
  44 }
  45
  46 static __inline__ __m512i __DEFAULT_FN_ATTRS
  47 _mm512_maskz_popcnt_epi64(__mmask8 __U, __m512i __A) {
  48   return _mm512_mask_popcnt_epi64((__m512i)_mm512_setzero_si512(), __U, __A);
  49 }
  50
  51 static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_popcnt_epi32(__m512i __A) {
  52   return (__m512i)__builtin_ia32_vpopcntd_512((__v16si)__A);
  53 }
  54
  55 static __inline__ __m512i __DEFAULT_FN_ATTRS
  56 _mm512_mask_popcnt_epi32(__m512i __W, __mmask16 __U, __m512i __A) {
  57   return (__m512i)__builtin_ia32_selectd_512(
  58       (__mmask16)__U, (__v16si)_mm512_popcnt_epi32(__A), (__v16si)__W);
  59 }
  60
  61 static __inline__ __m512i __DEFAULT_FN_ATTRS
  62 _mm512_maskz_popcnt_epi32(__mmask16 __U, __m512i __A) {
  63   return _mm512_mask_popcnt_epi32((__m512i)_mm512_setzero_si512(), __U, __A);
  64 }
  65
  66 #undef __DEFAULT_FN_ATTRS
  67
  68 #endif