113 lines · c
1/*===------------- avx512cdintrin.h - AVX512CD 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-exception7 *8 *===-----------------------------------------------------------------------===9 */10#ifndef __IMMINTRIN_H11#error "Never use <avx512cdintrin.h> directly; include <immintrin.h> instead."12#endif13 14#ifndef __AVX512CDINTRIN_H15#define __AVX512CDINTRIN_H16 17/* Define the default attributes for the functions in this file. */18#if defined(__cplusplus) && (__cplusplus >= 201103L)19#define __DEFAULT_FN_ATTRS \20 __attribute__((__always_inline__, __nodebug__, __target__("avx512cd"), \21 __min_vector_width__(512))) constexpr22#else23#define __DEFAULT_FN_ATTRS \24 __attribute__((__always_inline__, __nodebug__, __target__("avx512cd"), \25 __min_vector_width__(512)))26#endif27 28static __inline__ __m512i __DEFAULT_FN_ATTRS29_mm512_conflict_epi64(__m512i __A) {30 return (__m512i)__builtin_ia32_vpconflictdi_512((__v8di)__A);31}32 33static __inline__ __m512i __DEFAULT_FN_ATTRS34_mm512_mask_conflict_epi64(__m512i __W, __mmask8 __U, __m512i __A) {35 return (__m512i)__builtin_ia32_selectq_512(36 (__mmask8)__U, (__v8di)_mm512_conflict_epi64(__A), (__v8di)__W);37}38 39static __inline__ __m512i __DEFAULT_FN_ATTRS40_mm512_maskz_conflict_epi64(__mmask8 __U, __m512i __A) {41 return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,42 (__v8di)_mm512_conflict_epi64(__A),43 (__v8di)_mm512_setzero_si512());44}45 46static __inline__ __m512i __DEFAULT_FN_ATTRS47_mm512_conflict_epi32(__m512i __A) {48 return (__m512i)__builtin_ia32_vpconflictsi_512((__v16si)__A);49}50 51static __inline__ __m512i __DEFAULT_FN_ATTRS52_mm512_mask_conflict_epi32(__m512i __W, __mmask16 __U, __m512i __A) {53 return (__m512i)__builtin_ia32_selectd_512(54 (__mmask16)__U, (__v16si)_mm512_conflict_epi32(__A), (__v16si)__W);55}56 57static __inline__ __m512i __DEFAULT_FN_ATTRS58_mm512_maskz_conflict_epi32(__mmask16 __U, __m512i __A) {59 return (__m512i)__builtin_ia32_selectd_512(60 (__mmask16)__U, (__v16si)_mm512_conflict_epi32(__A),61 (__v16si)_mm512_setzero_si512());62}63 64static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_lzcnt_epi32(__m512i __A) {65 return (__m512i)__builtin_elementwise_clzg((__v16si)__A,66 (__v16si)_mm512_set1_epi32(32));67}68 69static __inline__ __m512i __DEFAULT_FN_ATTRS70_mm512_mask_lzcnt_epi32(__m512i __W, __mmask16 __U, __m512i __A) {71 return (__m512i)__builtin_ia32_selectd_512(72 (__mmask16)__U, (__v16si)_mm512_lzcnt_epi32(__A), (__v16si)__W);73}74 75static __inline__ __m512i __DEFAULT_FN_ATTRS76_mm512_maskz_lzcnt_epi32(__mmask16 __U, __m512i __A) {77 return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,78 (__v16si)_mm512_lzcnt_epi32(__A),79 (__v16si)_mm512_setzero_si512());80}81 82static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_lzcnt_epi64(__m512i __A) {83 return (__m512i)__builtin_elementwise_clzg(84 (__v8di)__A, (__v8di)_mm512_set1_epi64((long long)64));85}86 87static __inline__ __m512i __DEFAULT_FN_ATTRS88_mm512_mask_lzcnt_epi64(__m512i __W, __mmask8 __U, __m512i __A) {89 return (__m512i)__builtin_ia32_selectq_512(90 (__mmask8)__U, (__v8di)_mm512_lzcnt_epi64(__A), (__v8di)__W);91}92 93static __inline__ __m512i __DEFAULT_FN_ATTRS94_mm512_maskz_lzcnt_epi64(__mmask8 __U, __m512i __A) {95 return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,96 (__v8di)_mm512_lzcnt_epi64(__A),97 (__v8di)_mm512_setzero_si512());98}99 100static __inline__ __m512i __DEFAULT_FN_ATTRS101_mm512_broadcastmb_epi64(__mmask8 __A) {102 return (__m512i)_mm512_set1_epi64((long long)__A);103}104 105static __inline__ __m512i __DEFAULT_FN_ATTRS106_mm512_broadcastmw_epi32(__mmask16 __A) {107 return (__m512i)_mm512_set1_epi32((int)__A);108}109 110#undef __DEFAULT_FN_ATTRS111 112#endif113