1/*===------------------ vaesintrin.h - VAES 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 <vaesintrin.h> directly; include <immintrin.h> instead." 12#endif 13 14#ifndef __VAESINTRIN_H 15#define __VAESINTRIN_H 16 17/* Default attributes for YMM forms. */ 18#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("vaes"), __min_vector_width__(256))) 19 20/* Default attributes for ZMM forms. */ 21#define __DEFAULT_FN_ATTRS_F __attribute__((__always_inline__, __nodebug__, __target__("avx512f,vaes"), __min_vector_width__(512))) 22 23 24static __inline__ __m256i __DEFAULT_FN_ATTRS 25 _mm256_aesenc_epi128(__m256i __A, __m256i __B) 26{ 27 return (__m256i) __builtin_ia32_aesenc256((__v4di) __A, 28 (__v4di) __B); 29} 30 31static __inline__ __m256i __DEFAULT_FN_ATTRS 32 _mm256_aesdec_epi128(__m256i __A, __m256i __B) 33{ 34 return (__m256i) __builtin_ia32_aesdec256((__v4di) __A, 35 (__v4di) __B); 36} 37 38static __inline__ __m256i __DEFAULT_FN_ATTRS 39 _mm256_aesenclast_epi128(__m256i __A, __m256i __B) 40{ 41 return (__m256i) __builtin_ia32_aesenclast256((__v4di) __A, 42 (__v4di) __B); 43} 44 45static __inline__ __m256i __DEFAULT_FN_ATTRS 46 _mm256_aesdeclast_epi128(__m256i __A, __m256i __B) 47{ 48 return (__m256i) __builtin_ia32_aesdeclast256((__v4di) __A, 49 (__v4di) __B); 50} 51 52#ifdef __AVX512FINTRIN_H 53static __inline__ __m512i __DEFAULT_FN_ATTRS_F 54 _mm512_aesenc_epi128(__m512i __A, __m512i __B) 55{ 56 return (__m512i) __builtin_ia32_aesenc512((__v8di) __A, 57 (__v8di) __B); 58} 59 60static __inline__ __m512i __DEFAULT_FN_ATTRS_F 61 _mm512_aesdec_epi128(__m512i __A, __m512i __B) 62{ 63 return (__m512i) __builtin_ia32_aesdec512((__v8di) __A, 64 (__v8di) __B); 65} 66 67static __inline__ __m512i __DEFAULT_FN_ATTRS_F 68 _mm512_aesenclast_epi128(__m512i __A, __m512i __B) 69{ 70 return (__m512i) __builtin_ia32_aesenclast512((__v8di) __A, 71 (__v8di) __B); 72} 73 74static __inline__ __m512i __DEFAULT_FN_ATTRS_F 75 _mm512_aesdeclast_epi128(__m512i __A, __m512i __B) 76{ 77 return (__m512i) __builtin_ia32_aesdeclast512((__v8di) __A, 78 (__v8di) __B); 79} 80#endif // __AVX512FINTRIN_H 81 82#undef __DEFAULT_FN_ATTRS 83#undef __DEFAULT_FN_ATTRS_F 84 85#endif // __VAESINTRIN_H 86