vaesintrin.h 3.2 KB

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