test/CodeGen/fma4-builtins.c

   1 // RUN: %clang_cc1 %s -O3 -triple=x86_64-apple-darwin -target-feature +fma4 -emit-llvm -o - | FileCheck %s
   2
   3 // Don't include mm_malloc.h, it's system specific.
   4 #define __MM_MALLOC_H
   5
   6 #include <x86intrin.h>
   7
   8 __m128 test_mm_macc_ps(__m128 a, __m128 b, __m128 c) {
   9   // CHECK: @llvm.x86.fma.vfmadd.ps
  10   return _mm_macc_ps(a, b, c);
  11 }
  12
  13 __m128d test_mm_macc_pd(__m128d a, __m128d b, __m128d c) {
  14   // CHECK: @llvm.x86.fma.vfmadd.pd
  15   return _mm_macc_pd(a, b, c);
  16 }
  17
  18 __m128 test_mm_macc_ss(__m128 a, __m128 b, __m128 c) {
  19   // CHECK: @llvm.x86.fma.vfmadd.ss
  20   return _mm_macc_ss(a, b, c);
  21 }
  22
  23 __m128d test_mm_macc_sd(__m128d a, __m128d b, __m128d c) {
  24   // CHECK: @llvm.x86.fma.vfmadd.sd
  25   return _mm_macc_sd(a, b, c);
  26 }
  27
  28 __m128 test_mm_msub_ps(__m128 a, __m128 b, __m128 c) {
  29   // CHECK: @llvm.x86.fma.vfmsub.ps
  30   return _mm_msub_ps(a, b, c);
  31 }
  32
  33 __m128d test_mm_msub_pd(__m128d a, __m128d b, __m128d c) {
  34   // CHECK: @llvm.x86.fma.vfmsub.pd
  35   return _mm_msub_pd(a, b, c);
  36 }
  37
  38 __m128 test_mm_msub_ss(__m128 a, __m128 b, __m128 c) {
  39   // CHECK: @llvm.x86.fma.vfmsub.ss
  40   return _mm_msub_ss(a, b, c);
  41 }
  42
  43 __m128d test_mm_msub_sd(__m128d a, __m128d b, __m128d c) {
  44   // CHECK: @llvm.x86.fma.vfmsub.sd
  45   return _mm_msub_sd(a, b, c);
  46 }
  47
  48 __m128 test_mm_nmacc_ps(__m128 a, __m128 b, __m128 c) {
  49   // CHECK: @llvm.x86.fma.vfnmadd.ps
  50   return _mm_nmacc_ps(a, b, c);
  51 }
  52
  53 __m128d test_mm_nmacc_pd(__m128d a, __m128d b, __m128d c) {
  54   // CHECK: @llvm.x86.fma.vfnmadd.pd
  55   return _mm_nmacc_pd(a, b, c);
  56 }
  57
  58 __m128 test_mm_nmacc_ss(__m128 a, __m128 b, __m128 c) {
  59   // CHECK: @llvm.x86.fma.vfnmadd.ss
  60   return _mm_nmacc_ss(a, b, c);
  61 }
  62
  63 __m128d test_mm_nmacc_sd(__m128d a, __m128d b, __m128d c) {
  64   // CHECK: @llvm.x86.fma.vfnmadd.sd
  65   return _mm_nmacc_sd(a, b, c);
  66 }
  67
  68 __m128 test_mm_nmsub_ps(__m128 a, __m128 b, __m128 c) {
  69   // CHECK: @llvm.x86.fma.vfnmsub.ps
  70   return _mm_nmsub_ps(a, b, c);
  71 }
  72
  73 __m128d test_mm_nmsub_pd(__m128d a, __m128d b, __m128d c) {
  74   // CHECK: @llvm.x86.fma.vfnmsub.pd
  75   return _mm_nmsub_pd(a, b, c);
  76 }
  77
  78 __m128 test_mm_nmsub_ss(__m128 a, __m128 b, __m128 c) {
  79   // CHECK: @llvm.x86.fma.vfnmsub.ss
  80   return _mm_nmsub_ss(a, b, c);
  81 }
  82
  83 __m128d test_mm_nmsub_sd(__m128d a, __m128d b, __m128d c) {
  84   // CHECK: @llvm.x86.fma.vfnmsub.sd
  85   return _mm_nmsub_sd(a, b, c);
  86 }
  87
  88 __m128 test_mm_maddsub_ps(__m128 a, __m128 b, __m128 c) {
  89   // CHECK: @llvm.x86.fma.vfmaddsub.ps
  90   return _mm_maddsub_ps(a, b, c);
  91 }
  92
  93 __m128d test_mm_maddsub_pd(__m128d a, __m128d b, __m128d c) {
  94   // CHECK: @llvm.x86.fma.vfmaddsub.pd
  95   return _mm_maddsub_pd(a, b, c);
  96 }
  97
  98 __m128 test_mm_msubadd_ps(__m128 a, __m128 b, __m128 c) {
  99   // CHECK: @llvm.x86.fma.vfmsubadd.ps
 100   return _mm_msubadd_ps(a, b, c);
 101 }
 102
 103 __m128d test_mm_msubadd_pd(__m128d a, __m128d b, __m128d c) {
 104   // CHECK: @llvm.x86.fma.vfmsubadd.pd
 105   return _mm_msubadd_pd(a, b, c);
 106 }
 107
 108 __m256 test_mm256_macc_ps(__m256 a, __m256 b, __m256 c) {
 109   // CHECK: @llvm.x86.fma.vfmadd.ps.256
 110   return _mm256_macc_ps(a, b, c);
 111 }
 112
 113 __m256d test_mm256_macc_pd(__m256d a, __m256d b, __m256d c) {
 114   // CHECK: @llvm.x86.fma.vfmadd.pd.256
 115   return _mm256_macc_pd(a, b, c);
 116 }
 117
 118 __m256 test_mm256_msub_ps(__m256 a, __m256 b, __m256 c) {
 119   // CHECK: @llvm.x86.fma.vfmsub.ps.256
 120   return _mm256_msub_ps(a, b, c);
 121 }
 122
 123 __m256d test_mm256_msub_pd(__m256d a, __m256d b, __m256d c) {
 124   // CHECK: @llvm.x86.fma.vfmsub.pd.256
 125   return _mm256_msub_pd(a, b, c);
 126 }
 127
 128 __m256 test_mm256_nmacc_ps(__m256 a, __m256 b, __m256 c) {
 129   // CHECK: @llvm.x86.fma.vfnmadd.ps.256
 130   return _mm256_nmacc_ps(a, b, c);
 131 }
 132
 133 __m256d test_mm256_nmacc_pd(__m256d a, __m256d b, __m256d c) {
 134   // CHECK: @llvm.x86.fma.vfnmadd.pd.256
 135   return _mm256_nmacc_pd(a, b, c);
 136 }
 137
 138 __m256 test_mm256_nmsub_ps(__m256 a, __m256 b, __m256 c) {
 139   // CHECK: @llvm.x86.fma.vfnmsub.ps.256
 140   return _mm256_nmsub_ps(a, b, c);
 141 }
 142
 143 __m256d test_mm256_nmsub_pd(__m256d a, __m256d b, __m256d c) {
 144   // CHECK: @llvm.x86.fma.vfnmsub.pd.256
 145   return _mm256_nmsub_pd(a, b, c);
 146 }
 147
 148 __m256 test_mm256_maddsub_ps(__m256 a, __m256 b, __m256 c) {
 149   // CHECK: @llvm.x86.fma.vfmaddsub.ps.256
 150   return _mm256_maddsub_ps(a, b, c);
 151 }
 152
 153 __m256d test_mm256_maddsub_pd(__m256d a, __m256d b, __m256d c) {
 154   // CHECK: @llvm.x86.fma.vfmaddsub.pd.256
 155   return _mm256_maddsub_pd(a, b, c);
 156 }
 157
 158 __m256 test_mm256_msubadd_ps(__m256 a, __m256 b, __m256 c) {
 159   // CHECK: @llvm.x86.fma.vfmsubadd.ps.256
 160   return _mm256_msubadd_ps(a, b, c);
 161 }
 162
 163 __m256d test_mm256_msubadd_pd(__m256d a, __m256d b, __m256d c) {
 164   // CHECK: @llvm.x86.fma.vfmsubadd.pd.256
 165   return _mm256_msubadd_pd(a, b, c);
 166 }