test/CodeGen/X86/xop-intrinsics-fast-isel.ll

   1 ; NOTE: Assertions have been autogenerated by utils/update_llc_test_checks.py
   2 ; RUN: llc < %s -fast-isel -mtriple=i686-unknown-unknown -mattr=+avx,+fma4,+xop | FileCheck %s --check-prefix=ALL --check-prefix=X32
   3 ; RUN: llc < %s -fast-isel -mtriple=x86_64-unknown-unknown -mattr=+avx,+fma4,+xop | FileCheck %s --check-prefix=ALL --check-prefix=X64
   4
   5 ; NOTE: This should use IR equivalent to what is generated by clang/test/CodeGen/xop-builtins.c
   6
   7 define <2 x i64> @test_mm_maccs_epi16(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
   8 ; ALL-LABEL: test_mm_maccs_epi16:
   9 ; ALL:       # %bb.0:
  10 ; ALL-NEXT:    vpmacssww %xmm2, %xmm1, %xmm0, %xmm0
  11 ; ALL-NEXT:    ret{{[l|q]}}
  12   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
  13   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
  14   %arg2 = bitcast <2 x i64> %a2 to <8 x i16>
  15   %res = call <8 x i16> @llvm.x86.xop.vpmacssww(<8 x i16> %arg0, <8 x i16> %arg1, <8 x i16> %arg2)
  16   %bc = bitcast <8 x i16> %res to <2 x i64>
  17   ret <2 x i64> %bc
  18 }
  19 declare <8 x i16> @llvm.x86.xop.vpmacssww(<8 x i16>, <8 x i16>, <8 x i16>) nounwind readnone
  20
  21 define <2 x i64> @test_mm_macc_epi16(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
  22 ; ALL-LABEL: test_mm_macc_epi16:
  23 ; ALL:       # %bb.0:
  24 ; ALL-NEXT:    vpmacsww %xmm2, %xmm1, %xmm0, %xmm0
  25 ; ALL-NEXT:    ret{{[l|q]}}
  26   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
  27   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
  28   %arg2 = bitcast <2 x i64> %a2 to <8 x i16>
  29   %res = call <8 x i16> @llvm.x86.xop.vpmacsww(<8 x i16> %arg0, <8 x i16> %arg1, <8 x i16> %arg2)
  30   %bc = bitcast <8 x i16> %res to <2 x i64>
  31   ret <2 x i64> %bc
  32 }
  33 declare <8 x i16> @llvm.x86.xop.vpmacsww(<8 x i16>, <8 x i16>, <8 x i16>) nounwind readnone
  34
  35 define <2 x i64> @test_mm_maccsd_epi16(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
  36 ; ALL-LABEL: test_mm_maccsd_epi16:
  37 ; ALL:       # %bb.0:
  38 ; ALL-NEXT:    vpmacsswd %xmm2, %xmm1, %xmm0, %xmm0
  39 ; ALL-NEXT:    ret{{[l|q]}}
  40   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
  41   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
  42   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
  43   %res = call <4 x i32> @llvm.x86.xop.vpmacsswd(<8 x i16> %arg0, <8 x i16> %arg1, <4 x i32> %arg2)
  44   %bc = bitcast <4 x i32> %res to <2 x i64>
  45   ret <2 x i64> %bc
  46 }
  47 declare <4 x i32> @llvm.x86.xop.vpmacsswd(<8 x i16>, <8 x i16>, <4 x i32>) nounwind readnone
  48
  49 define <2 x i64> @test_mm_maccd_epi16(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
  50 ; ALL-LABEL: test_mm_maccd_epi16:
  51 ; ALL:       # %bb.0:
  52 ; ALL-NEXT:    vpmacswd %xmm2, %xmm1, %xmm0, %xmm0
  53 ; ALL-NEXT:    ret{{[l|q]}}
  54   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
  55   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
  56   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
  57   %res = call <4 x i32> @llvm.x86.xop.vpmacswd(<8 x i16> %arg0, <8 x i16> %arg1, <4 x i32> %arg2)
  58   %bc = bitcast <4 x i32> %res to <2 x i64>
  59   ret <2 x i64> %bc
  60 }
  61 declare <4 x i32> @llvm.x86.xop.vpmacswd(<8 x i16>, <8 x i16>, <4 x i32>) nounwind readnone
  62
  63 define <2 x i64> @test_mm_maccs_epi32(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
  64 ; ALL-LABEL: test_mm_maccs_epi32:
  65 ; ALL:       # %bb.0:
  66 ; ALL-NEXT:    vpmacssdd %xmm2, %xmm1, %xmm0, %xmm0
  67 ; ALL-NEXT:    ret{{[l|q]}}
  68   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
  69   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
  70   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
  71   %res = call <4 x i32> @llvm.x86.xop.vpmacssdd(<4 x i32> %arg0, <4 x i32> %arg1, <4 x i32> %arg2)
  72   %bc = bitcast <4 x i32> %res to <2 x i64>
  73   ret <2 x i64> %bc
  74 }
  75 declare <4 x i32> @llvm.x86.xop.vpmacssdd(<4 x i32>, <4 x i32>, <4 x i32>) nounwind readnone
  76
  77 define <2 x i64> @test_mm_macc_epi32(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
  78 ; ALL-LABEL: test_mm_macc_epi32:
  79 ; ALL:       # %bb.0:
  80 ; ALL-NEXT:    vpmacsdd %xmm2, %xmm1, %xmm0, %xmm0
  81 ; ALL-NEXT:    ret{{[l|q]}}
  82   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
  83   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
  84   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
  85   %res = call <4 x i32> @llvm.x86.xop.vpmacsdd(<4 x i32> %arg0, <4 x i32> %arg1, <4 x i32> %arg2)
  86   %bc = bitcast <4 x i32> %res to <2 x i64>
  87   ret <2 x i64> %bc
  88 }
  89 declare <4 x i32> @llvm.x86.xop.vpmacsdd(<4 x i32>, <4 x i32>, <4 x i32>) nounwind readnone
  90
  91 define <2 x i64> @test_mm_maccslo_epi32(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
  92 ; ALL-LABEL: test_mm_maccslo_epi32:
  93 ; ALL:       # %bb.0:
  94 ; ALL-NEXT:    vpmacssdql %xmm2, %xmm1, %xmm0, %xmm0
  95 ; ALL-NEXT:    ret{{[l|q]}}
  96   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
  97   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
  98   %res = call <2 x i64> @llvm.x86.xop.vpmacssdql(<4 x i32> %arg0, <4 x i32> %arg1, <2 x i64> %a2)
  99   ret <2 x i64> %res
 100 }
 101 declare <2 x i64> @llvm.x86.xop.vpmacssdql(<4 x i32>, <4 x i32>, <2 x i64>) nounwind readnone
 102
 103 define <2 x i64> @test_mm_macclo_epi32(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
 104 ; ALL-LABEL: test_mm_macclo_epi32:
 105 ; ALL:       # %bb.0:
 106 ; ALL-NEXT:    vpmacsdql %xmm2, %xmm1, %xmm0, %xmm0
 107 ; ALL-NEXT:    ret{{[l|q]}}
 108   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 109   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 110   %res = call <2 x i64> @llvm.x86.xop.vpmacsdql(<4 x i32> %arg0, <4 x i32> %arg1, <2 x i64> %a2)
 111   ret <2 x i64> %res
 112 }
 113 declare <2 x i64> @llvm.x86.xop.vpmacsdql(<4 x i32>, <4 x i32>, <2 x i64>) nounwind readnone
 114
 115 define <2 x i64> @test_mm_maccshi_epi32(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
 116 ; ALL-LABEL: test_mm_maccshi_epi32:
 117 ; ALL:       # %bb.0:
 118 ; ALL-NEXT:    vpmacssdqh %xmm2, %xmm1, %xmm0, %xmm0
 119 ; ALL-NEXT:    ret{{[l|q]}}
 120   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 121   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 122   %res = call <2 x i64> @llvm.x86.xop.vpmacssdqh(<4 x i32> %arg0, <4 x i32> %arg1, <2 x i64> %a2)
 123   ret <2 x i64> %res
 124 }
 125 declare <2 x i64> @llvm.x86.xop.vpmacssdqh(<4 x i32>, <4 x i32>, <2 x i64>) nounwind readnone
 126
 127 define <2 x i64> @test_mm_macchi_epi32(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
 128 ; ALL-LABEL: test_mm_macchi_epi32:
 129 ; ALL:       # %bb.0:
 130 ; ALL-NEXT:    vpmacsdqh %xmm2, %xmm1, %xmm0, %xmm0
 131 ; ALL-NEXT:    ret{{[l|q]}}
 132   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 133   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 134   %res = call <2 x i64> @llvm.x86.xop.vpmacsdqh(<4 x i32> %arg0, <4 x i32> %arg1, <2 x i64> %a2)
 135   ret <2 x i64> %res
 136 }
 137 declare <2 x i64> @llvm.x86.xop.vpmacsdqh(<4 x i32>, <4 x i32>, <2 x i64>) nounwind readnone
 138
 139 define <2 x i64> @test_mm_maddsd_epi16(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
 140 ; ALL-LABEL: test_mm_maddsd_epi16:
 141 ; ALL:       # %bb.0:
 142 ; ALL-NEXT:    vpmadcsswd %xmm2, %xmm1, %xmm0, %xmm0
 143 ; ALL-NEXT:    ret{{[l|q]}}
 144   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 145   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 146   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
 147   %res = call <4 x i32> @llvm.x86.xop.vpmadcsswd(<8 x i16> %arg0, <8 x i16> %arg1, <4 x i32> %arg2)
 148   %bc = bitcast <4 x i32> %res to <2 x i64>
 149   ret <2 x i64> %bc
 150 }
 151 declare <4 x i32> @llvm.x86.xop.vpmadcsswd(<8 x i16>, <8 x i16>, <4 x i32>) nounwind readnone
 152
 153 define <2 x i64> @test_mm_maddd_epi16(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) nounwind {
 154 ; ALL-LABEL: test_mm_maddd_epi16:
 155 ; ALL:       # %bb.0:
 156 ; ALL-NEXT:    vpmadcswd %xmm2, %xmm1, %xmm0, %xmm0
 157 ; ALL-NEXT:    ret{{[l|q]}}
 158   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 159   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 160   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
 161   %res = call <4 x i32> @llvm.x86.xop.vpmadcswd(<8 x i16> %arg0, <8 x i16> %arg1, <4 x i32> %arg2)
 162   %bc = bitcast <4 x i32> %res to <2 x i64>
 163   ret <2 x i64> %bc
 164 }
 165 declare <4 x i32> @llvm.x86.xop.vpmadcswd(<8 x i16>, <8 x i16>, <4 x i32>) nounwind readnone
 166
 167 define <2 x i64> @test_mm_haddw_epi8(<2 x i64> %a0) {
 168 ; ALL-LABEL: test_mm_haddw_epi8:
 169 ; ALL:       # %bb.0:
 170 ; ALL-NEXT:    vphaddbw %xmm0, %xmm0
 171 ; ALL-NEXT:    ret{{[l|q]}}
 172   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 173   %res = call <8 x i16> @llvm.x86.xop.vphaddbw(<16 x i8> %arg0)
 174   %bc = bitcast <8 x i16> %res to <2 x i64>
 175   ret <2 x i64> %bc
 176 }
 177 declare <8 x i16> @llvm.x86.xop.vphaddbw(<16 x i8>) nounwind readnone
 178
 179 define <2 x i64> @test_mm_haddd_epi8(<2 x i64> %a0) {
 180 ; ALL-LABEL: test_mm_haddd_epi8:
 181 ; ALL:       # %bb.0:
 182 ; ALL-NEXT:    vphaddbd %xmm0, %xmm0
 183 ; ALL-NEXT:    ret{{[l|q]}}
 184   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 185   %res = call <4 x i32> @llvm.x86.xop.vphaddbd(<16 x i8> %arg0)
 186   %bc = bitcast <4 x i32> %res to <2 x i64>
 187   ret <2 x i64> %bc
 188 }
 189 declare <4 x i32> @llvm.x86.xop.vphaddbd(<16 x i8>) nounwind readnone
 190
 191 define <2 x i64> @test_mm_haddq_epi8(<2 x i64> %a0) {
 192 ; ALL-LABEL: test_mm_haddq_epi8:
 193 ; ALL:       # %bb.0:
 194 ; ALL-NEXT:    vphaddbq %xmm0, %xmm0
 195 ; ALL-NEXT:    ret{{[l|q]}}
 196   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 197   %res = call <2 x i64> @llvm.x86.xop.vphaddbq(<16 x i8> %arg0)
 198   ret <2 x i64> %res
 199 }
 200 declare <2 x i64> @llvm.x86.xop.vphaddbq(<16 x i8>) nounwind readnone
 201
 202 define <2 x i64> @test_mm_haddd_epi16(<2 x i64> %a0) {
 203 ; ALL-LABEL: test_mm_haddd_epi16:
 204 ; ALL:       # %bb.0:
 205 ; ALL-NEXT:    vphaddwd %xmm0, %xmm0
 206 ; ALL-NEXT:    ret{{[l|q]}}
 207   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 208   %res = call <4 x i32> @llvm.x86.xop.vphaddwd(<8 x i16> %arg0)
 209   %bc = bitcast <4 x i32> %res to <2 x i64>
 210   ret <2 x i64> %bc
 211 }
 212 declare <4 x i32> @llvm.x86.xop.vphaddwd(<8 x i16>) nounwind readnone
 213
 214 define <2 x i64> @test_mm_haddq_epi16(<2 x i64> %a0) {
 215 ; ALL-LABEL: test_mm_haddq_epi16:
 216 ; ALL:       # %bb.0:
 217 ; ALL-NEXT:    vphaddwq %xmm0, %xmm0
 218 ; ALL-NEXT:    ret{{[l|q]}}
 219   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 220   %res = call <2 x i64> @llvm.x86.xop.vphaddwq(<8 x i16> %arg0)
 221   ret <2 x i64> %res
 222 }
 223 declare <2 x i64> @llvm.x86.xop.vphaddwq(<8 x i16>) nounwind readnone
 224
 225 define <2 x i64> @test_mm_haddq_epi32(<2 x i64> %a0) {
 226 ; ALL-LABEL: test_mm_haddq_epi32:
 227 ; ALL:       # %bb.0:
 228 ; ALL-NEXT:    vphadddq %xmm0, %xmm0
 229 ; ALL-NEXT:    ret{{[l|q]}}
 230   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 231   %res = call <2 x i64> @llvm.x86.xop.vphadddq(<4 x i32> %arg0)
 232   ret <2 x i64> %res
 233 }
 234 declare <2 x i64> @llvm.x86.xop.vphadddq(<4 x i32>) nounwind readnone
 235
 236 define <2 x i64> @test_mm_haddw_epu8(<2 x i64> %a0) {
 237 ; ALL-LABEL: test_mm_haddw_epu8:
 238 ; ALL:       # %bb.0:
 239 ; ALL-NEXT:    vphaddubw %xmm0, %xmm0
 240 ; ALL-NEXT:    ret{{[l|q]}}
 241   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 242   %res = call <8 x i16> @llvm.x86.xop.vphaddubw(<16 x i8> %arg0)
 243   %bc = bitcast <8 x i16> %res to <2 x i64>
 244   ret <2 x i64> %bc
 245 }
 246 declare <8 x i16> @llvm.x86.xop.vphaddubw(<16 x i8>) nounwind readnone
 247
 248 define <2 x i64> @test_mm_haddd_epu8(<2 x i64> %a0) {
 249 ; ALL-LABEL: test_mm_haddd_epu8:
 250 ; ALL:       # %bb.0:
 251 ; ALL-NEXT:    vphaddubd %xmm0, %xmm0
 252 ; ALL-NEXT:    ret{{[l|q]}}
 253   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 254   %res = call <4 x i32> @llvm.x86.xop.vphaddubd(<16 x i8> %arg0)
 255   %bc = bitcast <4 x i32> %res to <2 x i64>
 256   ret <2 x i64> %bc
 257 }
 258 declare <4 x i32> @llvm.x86.xop.vphaddubd(<16 x i8>) nounwind readnone
 259
 260 define <2 x i64> @test_mm_haddq_epu8(<2 x i64> %a0) {
 261 ; ALL-LABEL: test_mm_haddq_epu8:
 262 ; ALL:       # %bb.0:
 263 ; ALL-NEXT:    vphaddubq %xmm0, %xmm0
 264 ; ALL-NEXT:    ret{{[l|q]}}
 265   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 266   %res = call <2 x i64> @llvm.x86.xop.vphaddubq(<16 x i8> %arg0)
 267   ret <2 x i64> %res
 268 }
 269 declare <2 x i64> @llvm.x86.xop.vphaddubq(<16 x i8>) nounwind readnone
 270
 271 define <2 x i64> @test_mm_haddd_epu16(<2 x i64> %a0) {
 272 ; ALL-LABEL: test_mm_haddd_epu16:
 273 ; ALL:       # %bb.0:
 274 ; ALL-NEXT:    vphadduwd %xmm0, %xmm0
 275 ; ALL-NEXT:    ret{{[l|q]}}
 276   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 277   %res = call <4 x i32> @llvm.x86.xop.vphadduwd(<8 x i16> %arg0)
 278   %bc = bitcast <4 x i32> %res to <2 x i64>
 279   ret <2 x i64> %bc
 280 }
 281 declare <4 x i32> @llvm.x86.xop.vphadduwd(<8 x i16>) nounwind readnone
 282
 283
 284 define <2 x i64> @test_mm_haddq_epu16(<2 x i64> %a0) {
 285 ; ALL-LABEL: test_mm_haddq_epu16:
 286 ; ALL:       # %bb.0:
 287 ; ALL-NEXT:    vphadduwq %xmm0, %xmm0
 288 ; ALL-NEXT:    ret{{[l|q]}}
 289   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 290   %res = call <2 x i64> @llvm.x86.xop.vphadduwq(<8 x i16> %arg0)
 291   ret <2 x i64> %res
 292 }
 293 declare <2 x i64> @llvm.x86.xop.vphadduwq(<8 x i16>) nounwind readnone
 294
 295 define <2 x i64> @test_mm_haddq_epu32(<2 x i64> %a0) {
 296 ; ALL-LABEL: test_mm_haddq_epu32:
 297 ; ALL:       # %bb.0:
 298 ; ALL-NEXT:    vphaddudq %xmm0, %xmm0
 299 ; ALL-NEXT:    ret{{[l|q]}}
 300   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 301   %res = call <2 x i64> @llvm.x86.xop.vphaddudq(<4 x i32> %arg0)
 302   ret <2 x i64> %res
 303 }
 304 declare <2 x i64> @llvm.x86.xop.vphaddudq(<4 x i32>) nounwind readnone
 305
 306 define <2 x i64> @test_mm_hsubw_epi8(<2 x i64> %a0) {
 307 ; ALL-LABEL: test_mm_hsubw_epi8:
 308 ; ALL:       # %bb.0:
 309 ; ALL-NEXT:    vphsubbw %xmm0, %xmm0
 310 ; ALL-NEXT:    ret{{[l|q]}}
 311   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 312   %res = call <8 x i16> @llvm.x86.xop.vphsubbw(<16 x i8> %arg0)
 313   %bc = bitcast <8 x i16> %res to <2 x i64>
 314   ret <2 x i64> %bc
 315 }
 316 declare <8 x i16> @llvm.x86.xop.vphsubbw(<16 x i8>) nounwind readnone
 317
 318 define <2 x i64> @test_mm_hsubd_epi16(<2 x i64> %a0) {
 319 ; ALL-LABEL: test_mm_hsubd_epi16:
 320 ; ALL:       # %bb.0:
 321 ; ALL-NEXT:    vphsubwd %xmm0, %xmm0
 322 ; ALL-NEXT:    ret{{[l|q]}}
 323   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 324   %res = call <4 x i32> @llvm.x86.xop.vphsubwd(<8 x i16> %arg0)
 325   %bc = bitcast <4 x i32> %res to <2 x i64>
 326   ret <2 x i64> %bc
 327 }
 328 declare <4 x i32> @llvm.x86.xop.vphsubwd(<8 x i16>) nounwind readnone
 329
 330 define <2 x i64> @test_mm_hsubq_epi32(<2 x i64> %a0) {
 331 ; ALL-LABEL: test_mm_hsubq_epi32:
 332 ; ALL:       # %bb.0:
 333 ; ALL-NEXT:    vphsubdq %xmm0, %xmm0
 334 ; ALL-NEXT:    ret{{[l|q]}}
 335   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 336   %res = call <2 x i64> @llvm.x86.xop.vphsubdq(<4 x i32> %arg0)
 337   ret <2 x i64> %res
 338 }
 339 declare <2 x i64> @llvm.x86.xop.vphsubdq(<4 x i32>) nounwind readnone
 340
 341 define <2 x i64> @test_mm_cmov_si128(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) {
 342 ; ALL-LABEL: test_mm_cmov_si128:
 343 ; ALL:       # %bb.0:
 344 ; ALL-NEXT:    vpcmpeqd %xmm3, %xmm3, %xmm3
 345 ; ALL-NEXT:    vpxor %xmm3, %xmm2, %xmm3
 346 ; ALL-NEXT:    vpand %xmm2, %xmm0, %xmm0
 347 ; ALL-NEXT:    vpand %xmm3, %xmm1, %xmm1
 348 ; ALL-NEXT:    vpor %xmm1, %xmm0, %xmm0
 349 ; ALL-NEXT:    ret{{[l|q]}}
 350   %res = call <2 x i64> @llvm.x86.xop.vpcmov(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2)
 351   ret <2 x i64> %res
 352 }
 353 declare <2 x i64> @llvm.x86.xop.vpcmov(<2 x i64>, <2 x i64>, <2 x i64>) nounwind readnone
 354
 355 define <4 x i64> @test_mm256_cmov_si256(<4 x i64> %a0, <4 x i64> %a1, <4 x i64> %a2) {
 356 ; ALL-LABEL: test_mm256_cmov_si256:
 357 ; ALL:       # %bb.0:
 358 ; ALL-NEXT:    vxorps %xmm3, %xmm3, %xmm3
 359 ; ALL-NEXT:    vcmptrueps %ymm3, %ymm3, %ymm3
 360 ; ALL-NEXT:    vxorps %ymm3, %ymm2, %ymm3
 361 ; ALL-NEXT:    vandps %ymm2, %ymm0, %ymm0
 362 ; ALL-NEXT:    vandps %ymm3, %ymm1, %ymm1
 363 ; ALL-NEXT:    vorps %ymm1, %ymm0, %ymm0
 364 ; ALL-NEXT:    ret{{[l|q]}}
 365   %res = call <4 x i64> @llvm.x86.xop.vpcmov.256(<4 x i64> %a0, <4 x i64> %a1, <4 x i64> %a2)
 366   ret <4 x i64> %res
 367 }
 368 declare <4 x i64> @llvm.x86.xop.vpcmov.256(<4 x i64>, <4 x i64>, <4 x i64>) nounwind readnone
 369
 370 define <2 x i64> @test_mm_perm_epi8(<2 x i64> %a0, <2 x i64> %a1, <2 x i64> %a2) {
 371 ; ALL-LABEL: test_mm_perm_epi8:
 372 ; ALL:       # %bb.0:
 373 ; ALL-NEXT:    vpperm %xmm2, %xmm1, %xmm0, %xmm0
 374 ; ALL-NEXT:    ret{{[l|q]}}
 375   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 376   %arg1 = bitcast <2 x i64> %a1 to <16 x i8>
 377   %arg2 = bitcast <2 x i64> %a2 to <16 x i8>
 378   %res = call <16 x i8> @llvm.x86.xop.vpperm(<16 x i8> %arg0, <16 x i8> %arg1, <16 x i8> %arg2)
 379   %bc = bitcast <16 x i8> %res to <2 x i64>
 380   ret <2 x i64> %bc
 381 }
 382 declare <16 x i8> @llvm.x86.xop.vpperm(<16 x i8>, <16 x i8>, <16 x i8>) nounwind readnone
 383
 384 define <2 x i64> @test_mm_rot_epi8(<2 x i64> %a0, <2 x i64> %a1) {
 385 ; ALL-LABEL: test_mm_rot_epi8:
 386 ; ALL:       # %bb.0:
 387 ; ALL-NEXT:    vprotb %xmm1, %xmm0, %xmm0
 388 ; ALL-NEXT:    ret{{[l|q]}}
 389   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 390   %arg1 = bitcast <2 x i64> %a1 to <16 x i8>
 391   %res = call <16 x i8> @llvm.fshl.v16i8(<16 x i8> %arg0, <16 x i8> %arg0, <16 x i8> %arg1)
 392   %bc = bitcast <16 x i8> %res to <2 x i64>
 393   ret <2 x i64> %bc
 394 }
 395 declare <16 x i8> @llvm.fshl.v16i8(<16 x i8>, <16 x i8>, <16 x i8>) nounwind readnone
 396
 397 define <2 x i64> @test_mm_rot_epi16(<2 x i64> %a0, <2 x i64> %a1) {
 398 ; ALL-LABEL: test_mm_rot_epi16:
 399 ; ALL:       # %bb.0:
 400 ; ALL-NEXT:    vprotw %xmm1, %xmm0, %xmm0
 401 ; ALL-NEXT:    ret{{[l|q]}}
 402   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 403   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 404   %res = call <8 x i16> @llvm.fshl.v8i16(<8 x i16> %arg0, <8 x i16> %arg0, <8 x i16> %arg1)
 405   %bc = bitcast <8 x i16> %res to <2 x i64>
 406   ret <2 x i64> %bc
 407 }
 408 declare <8 x i16> @llvm.fshl.v8i16(<8 x i16>, <8 x i16>, <8 x i16>) nounwind readnone
 409
 410 define <2 x i64> @test_mm_rot_epi32(<2 x i64> %a0, <2 x i64> %a1) {
 411 ; ALL-LABEL: test_mm_rot_epi32:
 412 ; ALL:       # %bb.0:
 413 ; ALL-NEXT:    vprotd %xmm1, %xmm0, %xmm0
 414 ; ALL-NEXT:    ret{{[l|q]}}
 415   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 416   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 417   %res = call <4 x i32> @llvm.fshl.v4i32(<4 x i32> %arg0, <4 x i32> %arg0, <4 x i32> %arg1)
 418   %bc = bitcast <4 x i32> %res to <2 x i64>
 419   ret <2 x i64> %bc
 420 }
 421 declare <4 x i32> @llvm.fshl.v4i32(<4 x i32>, <4 x i32>, <4 x i32>) nounwind readnone
 422
 423 define <2 x i64> @test_mm_rot_epi64(<2 x i64> %a0, <2 x i64> %a1) {
 424 ; ALL-LABEL: test_mm_rot_epi64:
 425 ; ALL:       # %bb.0:
 426 ; ALL-NEXT:    vprotq %xmm1, %xmm0, %xmm0
 427 ; ALL-NEXT:    ret{{[l|q]}}
 428   %res = call <2 x i64> @llvm.fshl.v2i64(<2 x i64> %a0, <2 x i64> %a0, <2 x i64> %a1)
 429   ret <2 x i64> %res
 430 }
 431 declare <2 x i64> @llvm.fshl.v2i64(<2 x i64>, <2 x i64>, <2 x i64>) nounwind readnone
 432
 433 define <2 x i64> @test_mm_roti_epi8(<2 x i64> %a0) {
 434 ; ALL-LABEL: test_mm_roti_epi8:
 435 ; ALL:       # %bb.0:
 436 ; ALL-NEXT:    vprotb $1, %xmm0, %xmm0
 437 ; ALL-NEXT:    ret{{[l|q]}}
 438   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 439   %res = call <16 x i8> @llvm.fshl.v16i8(<16 x i8> %arg0, <16 x i8> %arg0, <16 x i8> <i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1, i8 1>)
 440   %bc = bitcast <16 x i8> %res to <2 x i64>
 441   ret <2 x i64> %bc
 442 }
 443
 444 define <2 x i64> @test_mm_roti_epi16(<2 x i64> %a0) {
 445 ; ALL-LABEL: test_mm_roti_epi16:
 446 ; ALL:       # %bb.0:
 447 ; ALL-NEXT:    vprotw $2, %xmm0, %xmm0
 448 ; ALL-NEXT:    ret{{[l|q]}}
 449   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 450   %res = call <8 x i16> @llvm.fshl.v8i16(<8 x i16> %arg0, <8 x i16> %arg0, <8 x i16> <i16 50, i16 50, i16 50, i16 50, i16 50, i16 50, i16 50, i16 50>)
 451   %bc = bitcast <8 x i16> %res to <2 x i64>
 452   ret <2 x i64> %bc
 453 }
 454
 455 define <2 x i64> @test_mm_roti_epi32(<2 x i64> %a0) {
 456 ; ALL-LABEL: test_mm_roti_epi32:
 457 ; ALL:       # %bb.0:
 458 ; ALL-NEXT:    vprotd $2, %xmm0, %xmm0
 459 ; ALL-NEXT:    ret{{[l|q]}}
 460   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 461   %res = call <4 x i32> @llvm.fshl.v4i32(<4 x i32> %arg0, <4 x i32> %arg0, <4 x i32> <i32 -30, i32 -30, i32 -30, i32 -30>)
 462   %bc = bitcast <4 x i32> %res to <2 x i64>
 463   ret <2 x i64> %bc
 464 }
 465
 466 define <2 x i64> @test_mm_roti_epi64(<2 x i64> %a0) {
 467 ; ALL-LABEL: test_mm_roti_epi64:
 468 ; ALL:       # %bb.0:
 469 ; ALL-NEXT:    vprotq $36, %xmm0, %xmm0
 470 ; ALL-NEXT:    ret{{[l|q]}}
 471   %res = call <2 x i64> @llvm.fshl.v2i64(<2 x i64> %a0, <2 x i64> %a0, <2 x i64> <i64 100, i64 100>)
 472   ret <2 x i64> %res
 473 }
 474
 475 define <2 x i64> @test_mm_shl_epi8(<2 x i64> %a0, <2 x i64> %a1) {
 476 ; ALL-LABEL: test_mm_shl_epi8:
 477 ; ALL:       # %bb.0:
 478 ; ALL-NEXT:    vpshlb %xmm1, %xmm0, %xmm0
 479 ; ALL-NEXT:    ret{{[l|q]}}
 480   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 481   %arg1 = bitcast <2 x i64> %a1 to <16 x i8>
 482   %res = call <16 x i8> @llvm.x86.xop.vpshlb(<16 x i8> %arg0, <16 x i8> %arg1)
 483   %bc = bitcast <16 x i8> %res to <2 x i64>
 484   ret <2 x i64> %bc
 485 }
 486 declare <16 x i8> @llvm.x86.xop.vpshlb(<16 x i8>, <16 x i8>) nounwind readnone
 487
 488 define <2 x i64> @test_mm_shl_epi16(<2 x i64> %a0, <2 x i64> %a1) {
 489 ; ALL-LABEL: test_mm_shl_epi16:
 490 ; ALL:       # %bb.0:
 491 ; ALL-NEXT:    vpshlw %xmm1, %xmm0, %xmm0
 492 ; ALL-NEXT:    ret{{[l|q]}}
 493   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 494   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 495   %res = call <8 x i16> @llvm.x86.xop.vpshlw(<8 x i16> %arg0, <8 x i16> %arg1)
 496   %bc = bitcast <8 x i16> %res to <2 x i64>
 497   ret <2 x i64> %bc
 498 }
 499 declare <8 x i16> @llvm.x86.xop.vpshlw(<8 x i16>, <8 x i16>) nounwind readnone
 500
 501 define <2 x i64> @test_mm_shl_epi32(<2 x i64> %a0, <2 x i64> %a1) {
 502 ; ALL-LABEL: test_mm_shl_epi32:
 503 ; ALL:       # %bb.0:
 504 ; ALL-NEXT:    vpshld %xmm1, %xmm0, %xmm0
 505 ; ALL-NEXT:    ret{{[l|q]}}
 506   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 507   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 508   %res = call <4 x i32> @llvm.x86.xop.vpshld(<4 x i32> %arg0, <4 x i32> %arg1)
 509   %bc = bitcast <4 x i32> %res to <2 x i64>
 510   ret <2 x i64> %bc
 511 }
 512 declare <4 x i32> @llvm.x86.xop.vpshld(<4 x i32>, <4 x i32>) nounwind readnone
 513
 514 define <2 x i64> @test_mm_shl_epi64(<2 x i64> %a0, <2 x i64> %a1) {
 515 ; ALL-LABEL: test_mm_shl_epi64:
 516 ; ALL:       # %bb.0:
 517 ; ALL-NEXT:    vpshlq %xmm1, %xmm0, %xmm0
 518 ; ALL-NEXT:    ret{{[l|q]}}
 519   %res = call <2 x i64> @llvm.x86.xop.vpshlq(<2 x i64> %a0, <2 x i64> %a1)
 520   ret <2 x i64> %res
 521 }
 522 declare <2 x i64> @llvm.x86.xop.vpshlq(<2 x i64>, <2 x i64>) nounwind readnone
 523
 524 define <2 x i64> @test_mm_sha_epi8(<2 x i64> %a0, <2 x i64> %a1) {
 525 ; ALL-LABEL: test_mm_sha_epi8:
 526 ; ALL:       # %bb.0:
 527 ; ALL-NEXT:    vpshab %xmm1, %xmm0, %xmm0
 528 ; ALL-NEXT:    ret{{[l|q]}}
 529   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 530   %arg1 = bitcast <2 x i64> %a1 to <16 x i8>
 531   %res = call <16 x i8> @llvm.x86.xop.vpshab(<16 x i8> %arg0, <16 x i8> %arg1)
 532   %bc = bitcast <16 x i8> %res to <2 x i64>
 533   ret <2 x i64> %bc
 534 }
 535 declare <16 x i8> @llvm.x86.xop.vpshab(<16 x i8>, <16 x i8>) nounwind readnone
 536
 537 define <2 x i64> @test_mm_sha_epi16(<2 x i64> %a0, <2 x i64> %a1) {
 538 ; ALL-LABEL: test_mm_sha_epi16:
 539 ; ALL:       # %bb.0:
 540 ; ALL-NEXT:    vpshaw %xmm1, %xmm0, %xmm0
 541 ; ALL-NEXT:    ret{{[l|q]}}
 542   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 543   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 544   %res = call <8 x i16> @llvm.x86.xop.vpshaw(<8 x i16> %arg0, <8 x i16> %arg1)
 545   %bc = bitcast <8 x i16> %res to <2 x i64>
 546   ret <2 x i64> %bc
 547 }
 548 declare <8 x i16> @llvm.x86.xop.vpshaw(<8 x i16>, <8 x i16>) nounwind readnone
 549
 550 define <2 x i64> @test_mm_sha_epi32(<2 x i64> %a0, <2 x i64> %a1) {
 551 ; ALL-LABEL: test_mm_sha_epi32:
 552 ; ALL:       # %bb.0:
 553 ; ALL-NEXT:    vpshad %xmm1, %xmm0, %xmm0
 554 ; ALL-NEXT:    ret{{[l|q]}}
 555   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 556   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 557   %res = call <4 x i32> @llvm.x86.xop.vpshad(<4 x i32> %arg0, <4 x i32> %arg1)
 558   %bc = bitcast <4 x i32> %res to <2 x i64>
 559   ret <2 x i64> %bc
 560 }
 561 declare <4 x i32> @llvm.x86.xop.vpshad(<4 x i32>, <4 x i32>) nounwind readnone
 562
 563 define <2 x i64> @test_mm_sha_epi64(<2 x i64> %a0, <2 x i64> %a1) {
 564 ; ALL-LABEL: test_mm_sha_epi64:
 565 ; ALL:       # %bb.0:
 566 ; ALL-NEXT:    vpshaq %xmm1, %xmm0, %xmm0
 567 ; ALL-NEXT:    ret{{[l|q]}}
 568   %res = call <2 x i64> @llvm.x86.xop.vpshaq(<2 x i64> %a0, <2 x i64> %a1)
 569   ret <2 x i64> %res
 570 }
 571 declare <2 x i64> @llvm.x86.xop.vpshaq(<2 x i64>, <2 x i64>) nounwind readnone
 572
 573 define <2 x i64> @test_mm_com_epu8(<2 x i64> %a0, <2 x i64> %a1) {
 574 ; ALL-LABEL: test_mm_com_epu8:
 575 ; ALL:       # %bb.0:
 576 ; ALL-NEXT:    vpcomltub %xmm1, %xmm0, %xmm0
 577 ; ALL-NEXT:    ret{{[l|q]}}
 578   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 579   %arg1 = bitcast <2 x i64> %a1 to <16 x i8>
 580   %cmp = icmp ult <16 x i8> %arg0, %arg1
 581   %res = sext <16 x i1> %cmp to <16 x i8>
 582   %bc = bitcast <16 x i8> %res to <2 x i64>
 583   ret <2 x i64> %bc
 584 }
 585
 586 define <2 x i64> @test_mm_com_epu16(<2 x i64> %a0, <2 x i64> %a1) {
 587 ; ALL-LABEL: test_mm_com_epu16:
 588 ; ALL:       # %bb.0:
 589 ; ALL-NEXT:    vpcomltuw %xmm1, %xmm0, %xmm0
 590 ; ALL-NEXT:    ret{{[l|q]}}
 591   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 592   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 593   %cmp = icmp ult <8 x i16> %arg0, %arg1
 594   %res = sext <8 x i1> %cmp to <8 x i16>
 595   %bc = bitcast <8 x i16> %res to <2 x i64>
 596   ret <2 x i64> %bc
 597 }
 598
 599 define <2 x i64> @test_mm_com_epu32(<2 x i64> %a0, <2 x i64> %a1) {
 600 ; ALL-LABEL: test_mm_com_epu32:
 601 ; ALL:       # %bb.0:
 602 ; ALL-NEXT:    vpcomltud %xmm1, %xmm0, %xmm0
 603 ; ALL-NEXT:    ret{{[l|q]}}
 604   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 605   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 606   %cmp = icmp ult <4 x i32> %arg0, %arg1
 607   %res = sext <4 x i1> %cmp to <4 x i32>
 608   %bc = bitcast <4 x i32> %res to <2 x i64>
 609   ret <2 x i64> %bc
 610 }
 611
 612 define <2 x i64> @test_mm_com_epu64(<2 x i64> %a0, <2 x i64> %a1) {
 613 ; ALL-LABEL: test_mm_com_epu64:
 614 ; ALL:       # %bb.0:
 615 ; ALL-NEXT:    vpcomltuq %xmm1, %xmm0, %xmm0
 616 ; ALL-NEXT:    ret{{[l|q]}}
 617   %cmp = icmp ult <2 x i64> %a0, %a1
 618   %res = sext <2 x i1> %cmp to <2 x i64>
 619   ret <2 x i64> %res
 620 }
 621
 622 define <2 x i64> @test_mm_com_epi8(<2 x i64> %a0, <2 x i64> %a1) {
 623 ; ALL-LABEL: test_mm_com_epi8:
 624 ; ALL:       # %bb.0:
 625 ; ALL-NEXT:    vpcomltb %xmm1, %xmm0, %xmm0
 626 ; ALL-NEXT:    ret{{[l|q]}}
 627   %arg0 = bitcast <2 x i64> %a0 to <16 x i8>
 628   %arg1 = bitcast <2 x i64> %a1 to <16 x i8>
 629   %cmp = icmp slt <16 x i8> %arg0, %arg1
 630   %res = sext <16 x i1> %cmp to <16 x i8>
 631   %bc = bitcast <16 x i8> %res to <2 x i64>
 632   ret <2 x i64> %bc
 633 }
 634
 635 define <2 x i64> @test_mm_com_epi16(<2 x i64> %a0, <2 x i64> %a1) {
 636 ; ALL-LABEL: test_mm_com_epi16:
 637 ; ALL:       # %bb.0:
 638 ; ALL-NEXT:    vpcomltw %xmm1, %xmm0, %xmm0
 639 ; ALL-NEXT:    ret{{[l|q]}}
 640   %arg0 = bitcast <2 x i64> %a0 to <8 x i16>
 641   %arg1 = bitcast <2 x i64> %a1 to <8 x i16>
 642   %cmp = icmp slt <8 x i16> %arg0, %arg1
 643   %res = sext <8 x i1> %cmp to <8 x i16>
 644   %bc = bitcast <8 x i16> %res to <2 x i64>
 645   ret <2 x i64> %bc
 646 }
 647
 648 define <2 x i64> @test_mm_com_epi32(<2 x i64> %a0, <2 x i64> %a1) {
 649 ; ALL-LABEL: test_mm_com_epi32:
 650 ; ALL:       # %bb.0:
 651 ; ALL-NEXT:    vpcomltd %xmm1, %xmm0, %xmm0
 652 ; ALL-NEXT:    ret{{[l|q]}}
 653   %arg0 = bitcast <2 x i64> %a0 to <4 x i32>
 654   %arg1 = bitcast <2 x i64> %a1 to <4 x i32>
 655   %cmp = icmp slt <4 x i32> %arg0, %arg1
 656   %res = sext <4 x i1> %cmp to <4 x i32>
 657   %bc = bitcast <4 x i32> %res to <2 x i64>
 658   ret <2 x i64> %bc
 659 }
 660
 661 define <2 x i64> @test_mm_com_epi64(<2 x i64> %a0, <2 x i64> %a1) {
 662 ; ALL-LABEL: test_mm_com_epi64:
 663 ; ALL:       # %bb.0:
 664 ; ALL-NEXT:    vpcomltq %xmm1, %xmm0, %xmm0
 665 ; ALL-NEXT:    ret{{[l|q]}}
 666   %cmp = icmp slt <2 x i64> %a0, %a1
 667   %res = sext <2 x i1> %cmp to <2 x i64>
 668   ret <2 x i64> %res
 669 }
 670
 671 define <2 x double> @test_mm_permute2_pd(<2 x double> %a0, <2 x double> %a1, <2 x i64> %a2) {
 672 ; ALL-LABEL: test_mm_permute2_pd:
 673 ; ALL:       # %bb.0:
 674 ; ALL-NEXT:    vpermil2pd $0, %xmm2, %xmm1, %xmm0, %xmm0
 675 ; ALL-NEXT:    ret{{[l|q]}}
 676   %res = call <2 x double> @llvm.x86.xop.vpermil2pd(<2 x double> %a0, <2 x double> %a1, <2 x i64> %a2, i8 0)
 677   ret <2 x double> %res
 678 }
 679 declare <2 x double> @llvm.x86.xop.vpermil2pd(<2 x double>, <2 x double>, <2 x i64>, i8) nounwind readnone
 680
 681 define <4 x double> @test_mm256_permute2_pd(<4 x double> %a0, <4 x double> %a1, <4 x i64> %a2) {
 682 ; ALL-LABEL: test_mm256_permute2_pd:
 683 ; ALL:       # %bb.0:
 684 ; ALL-NEXT:    vpermil2pd $0, %ymm2, %ymm1, %ymm0, %ymm0
 685 ; ALL-NEXT:    ret{{[l|q]}}
 686   %res = call <4 x double> @llvm.x86.xop.vpermil2pd.256(<4 x double> %a0, <4 x double> %a1, <4 x i64> %a2, i8 0)
 687   ret <4 x double> %res
 688 }
 689 declare <4 x double> @llvm.x86.xop.vpermil2pd.256(<4 x double>, <4 x double>, <4 x i64>, i8) nounwind readnone
 690
 691 define <4 x float> @test_mm_permute2_ps(<4 x float> %a0, <4 x float> %a1, <2 x i64> %a2) {
 692 ; ALL-LABEL: test_mm_permute2_ps:
 693 ; ALL:       # %bb.0:
 694 ; ALL-NEXT:    vpermil2ps $0, %xmm2, %xmm1, %xmm0, %xmm0
 695 ; ALL-NEXT:    ret{{[l|q]}}
 696   %arg2 = bitcast <2 x i64> %a2 to <4 x i32>
 697   %res = call <4 x float> @llvm.x86.xop.vpermil2ps(<4 x float> %a0, <4 x float> %a1, <4 x i32> %arg2, i8 0)
 698   ret <4 x float> %res
 699 }
 700 declare <4 x float> @llvm.x86.xop.vpermil2ps(<4 x float>, <4 x float>, <4 x i32>, i8) nounwind readnone
 701
 702 define <8 x float> @test_mm256_permute2_ps(<8 x float> %a0, <8 x float> %a1, <4 x i64> %a2) {
 703 ; ALL-LABEL: test_mm256_permute2_ps:
 704 ; ALL:       # %bb.0:
 705 ; ALL-NEXT:    vpermil2ps $0, %ymm2, %ymm1, %ymm0, %ymm0
 706 ; ALL-NEXT:    ret{{[l|q]}}
 707   %arg2 = bitcast <4 x i64> %a2 to <8 x i32>
 708   %res = call <8 x float> @llvm.x86.xop.vpermil2ps.256(<8 x float> %a0, <8 x float> %a1, <8 x i32> %arg2, i8 0)
 709   ret <8 x float> %res
 710 }
 711 declare <8 x float> @llvm.x86.xop.vpermil2ps.256(<8 x float>, <8 x float>, <8 x i32>, i8) nounwind readnone
 712
 713 define <4 x float> @test_mm_frcz_ss(<4 x float> %a0) {
 714 ; ALL-LABEL: test_mm_frcz_ss:
 715 ; ALL:       # %bb.0:
 716 ; ALL-NEXT:    vfrczss %xmm0, %xmm0
 717 ; ALL-NEXT:    ret{{[l|q]}}
 718   %res = call <4 x float> @llvm.x86.xop.vfrcz.ss(<4 x float> %a0)
 719   ret <4 x float> %res
 720 }
 721 declare <4 x float> @llvm.x86.xop.vfrcz.ss(<4 x float>) nounwind readnone
 722
 723 define <2 x double> @test_mm_frcz_sd(<2 x double> %a0) {
 724 ; ALL-LABEL: test_mm_frcz_sd:
 725 ; ALL:       # %bb.0:
 726 ; ALL-NEXT:    vfrczsd %xmm0, %xmm0
 727 ; ALL-NEXT:    ret{{[l|q]}}
 728   %res = call <2 x double> @llvm.x86.xop.vfrcz.sd(<2 x double> %a0)
 729   ret <2 x double> %res
 730 }
 731 declare <2 x double> @llvm.x86.xop.vfrcz.sd(<2 x double>) nounwind readnone
 732
 733 define <4 x float> @test_mm_frcz_ps(<4 x float> %a0) {
 734 ; ALL-LABEL: test_mm_frcz_ps:
 735 ; ALL:       # %bb.0:
 736 ; ALL-NEXT:    vfrczps %xmm0, %xmm0
 737 ; ALL-NEXT:    ret{{[l|q]}}
 738   %res = call <4 x float> @llvm.x86.xop.vfrcz.ps(<4 x float> %a0)
 739   ret <4 x float> %res
 740 }
 741 declare <4 x float> @llvm.x86.xop.vfrcz.ps(<4 x float>) nounwind readnone
 742
 743 define <2 x double> @test_mm_frcz_pd(<2 x double> %a0) {
 744 ; ALL-LABEL: test_mm_frcz_pd:
 745 ; ALL:       # %bb.0:
 746 ; ALL-NEXT:    vfrczpd %xmm0, %xmm0
 747 ; ALL-NEXT:    ret{{[l|q]}}
 748   %res = call <2 x double> @llvm.x86.xop.vfrcz.pd(<2 x double> %a0)
 749   ret <2 x double> %res
 750 }
 751 declare <2 x double> @llvm.x86.xop.vfrcz.pd(<2 x double>) nounwind readnone
 752
 753 define <8 x float> @test_mm256_frcz_ps(<8 x float> %a0) {
 754 ; ALL-LABEL: test_mm256_frcz_ps:
 755 ; ALL:       # %bb.0:
 756 ; ALL-NEXT:    vfrczps %ymm0, %ymm0
 757 ; ALL-NEXT:    ret{{[l|q]}}
 758   %res = call <8 x float> @llvm.x86.xop.vfrcz.ps.256(<8 x float> %a0)
 759   ret <8 x float> %res
 760 }
 761 declare <8 x float> @llvm.x86.xop.vfrcz.ps.256(<8 x float>) nounwind readnone
 762
 763 define <4 x double> @test_mm256_frcz_pd(<4 x double> %a0) {
 764 ; ALL-LABEL: test_mm256_frcz_pd:
 765 ; ALL:       # %bb.0:
 766 ; ALL-NEXT:    vfrczpd %ymm0, %ymm0
 767 ; ALL-NEXT:    ret{{[l|q]}}
 768   %res = call <4 x double> @llvm.x86.xop.vfrcz.pd.256(<4 x double> %a0)
 769   ret <4 x double> %res
 770 }
 771 declare <4 x double> @llvm.x86.xop.vfrcz.pd.256(<4 x double>) nounwind readnone