llvm/test/CodeGen/ARM/arm-vld1.ll

   1 ; RUN: llc < %s -mtriple=armv8-linux-gnueabi -verify-machineinstrs \
   2 ; RUN:     -asm-verbose=false | FileCheck %s
   3
   4 %struct.uint16x4x2_t = type { <4 x i16>, <4 x i16> }
   5 %struct.uint16x4x3_t = type { <4 x i16>, <4 x i16>, <4 x i16> }
   6 %struct.uint16x4x4_t = type { <4 x i16>, <4 x i16>, <4 x i16>, <4 x i16> }
   7
   8 %struct.uint32x2x2_t = type { <2 x i32>, <2 x i32> }
   9 %struct.uint32x2x3_t = type { <2 x i32>, <2 x i32>, <2 x i32> }
  10 %struct.uint32x2x4_t = type { <2 x i32>, <2 x i32>, <2 x i32>, <2 x i32> }
  11
  12 %struct.uint64x1x2_t = type { <1 x i64>, <1 x i64> }
  13 %struct.uint64x1x3_t = type { <1 x i64>, <1 x i64>, <1 x i64> }
  14 %struct.uint64x1x4_t = type { <1 x i64>, <1 x i64>, <1 x i64>, <1 x i64> }
  15
  16 %struct.uint8x8x2_t = type { <8 x i8>, <8 x i8> }
  17 %struct.uint8x8x3_t = type { <8 x i8>, <8 x i8>, <8 x i8> }
  18 %struct.uint8x8x4_t = type { <8 x i8>, <8 x i8>, <8 x i8>, <8 x i8> }
  19
  20 %struct.uint16x8x2_t = type { <8 x i16>, <8 x i16> }
  21 %struct.uint16x8x3_t = type { <8 x i16>, <8 x i16>, <8 x i16> }
  22 %struct.uint16x8x4_t = type { <8 x i16>, <8 x i16>, <8 x i16>, <8 x i16> }
  23
  24 %struct.uint32x4x2_t = type { <4 x i32>, <4 x i32> }
  25 %struct.uint32x4x3_t = type { <4 x i32>, <4 x i32>, <4 x i32> }
  26 %struct.uint32x4x4_t = type { <4 x i32>, <4 x i32>, <4 x i32>, <4 x i32> }
  27
  28 %struct.uint64x2x2_t = type { <2 x i64>, <2 x i64> }
  29 %struct.uint64x2x3_t = type { <2 x i64>, <2 x i64>, <2 x i64> }
  30 %struct.uint64x2x4_t = type { <2 x i64>, <2 x i64>, <2 x i64>, <2 x i64> }
  31
  32 %struct.uint8x16x2_t = type { <16 x i8>, <16 x i8> }
  33 %struct.uint8x16x3_t = type { <16 x i8>, <16 x i8>, <16 x i8> }
  34 %struct.uint8x16x4_t = type { <16 x i8>, <16 x i8>, <16 x i8>, <16 x i8> }
  35
  36 declare %struct.uint16x4x2_t @llvm.arm.neon.vld1x2.v4i16.p0(ptr) nounwind readonly
  37 declare %struct.uint16x4x3_t @llvm.arm.neon.vld1x3.v4i16.p0(ptr) nounwind readonly
  38 declare %struct.uint16x4x4_t @llvm.arm.neon.vld1x4.v4i16.p0(ptr) nounwind readonly
  39
  40 declare %struct.uint32x2x2_t @llvm.arm.neon.vld1x2.v2i32.p0(ptr) nounwind readonly
  41 declare %struct.uint32x2x3_t @llvm.arm.neon.vld1x3.v2i32.p0(ptr) nounwind readonly
  42 declare %struct.uint32x2x4_t @llvm.arm.neon.vld1x4.v2i32.p0(ptr) nounwind readonly
  43
  44 declare %struct.uint64x1x2_t @llvm.arm.neon.vld1x2.v1i64.p0(ptr) nounwind readonly
  45 declare %struct.uint64x1x3_t @llvm.arm.neon.vld1x3.v1i64.p0(ptr) nounwind readonly
  46 declare %struct.uint64x1x4_t @llvm.arm.neon.vld1x4.v1i64.p0(ptr) nounwind readonly
  47
  48 declare %struct.uint8x8x2_t @llvm.arm.neon.vld1x2.v8i8.p0(ptr) nounwind readonly
  49 declare %struct.uint8x8x3_t @llvm.arm.neon.vld1x3.v8i8.p0(ptr) nounwind readonly
  50 declare %struct.uint8x8x4_t @llvm.arm.neon.vld1x4.v8i8.p0(ptr) nounwind readonly
  51
  52 declare %struct.uint16x8x2_t @llvm.arm.neon.vld1x2.v8i16.p0(ptr) nounwind readonly
  53 declare %struct.uint16x8x3_t @llvm.arm.neon.vld1x3.v8i16.p0(ptr) nounwind readonly
  54 declare %struct.uint16x8x4_t @llvm.arm.neon.vld1x4.v8i16.p0(ptr) nounwind readonly
  55
  56 declare %struct.uint32x4x2_t @llvm.arm.neon.vld1x2.v4i32.p0(ptr) nounwind readonly
  57 declare %struct.uint32x4x3_t @llvm.arm.neon.vld1x3.v4i32.p0(ptr) nounwind readonly
  58 declare %struct.uint32x4x4_t @llvm.arm.neon.vld1x4.v4i32.p0(ptr) nounwind readonly
  59
  60 declare %struct.uint64x2x2_t @llvm.arm.neon.vld1x2.v2i64.p0(ptr) nounwind readonly
  61 declare %struct.uint64x2x3_t @llvm.arm.neon.vld1x3.v2i64.p0(ptr) nounwind readonly
  62 declare %struct.uint64x2x4_t @llvm.arm.neon.vld1x4.v2i64.p0(ptr) nounwind readonly
  63
  64 declare %struct.uint8x16x2_t @llvm.arm.neon.vld1x2.v16i8.p0(ptr) nounwind readonly
  65 declare %struct.uint8x16x3_t @llvm.arm.neon.vld1x3.v16i8.p0(ptr) nounwind readonly
  66 declare %struct.uint8x16x4_t @llvm.arm.neon.vld1x4.v16i8.p0(ptr) nounwind readonly
  67
  68 ; CHECK-LABEL: test_vld1_u16_x2
  69 ; CHECK: vld1.16 {d16, d17}, [r0:64]
  70 define %struct.uint16x4x2_t @test_vld1_u16_x2(ptr %a) nounwind {
  71   %tmp = tail call %struct.uint16x4x2_t @llvm.arm.neon.vld1x2.v4i16.p0(ptr %a)
  72   ret %struct.uint16x4x2_t %tmp
  73 }
  74
  75 ; CHECK-LABEL: test_vld1_u16_x3
  76 ; CHECK: vld1.16 {d16, d17, d18}, [r1:64]
  77 define %struct.uint16x4x3_t @test_vld1_u16_x3(ptr %a) nounwind {
  78   %tmp = tail call %struct.uint16x4x3_t @llvm.arm.neon.vld1x3.v4i16.p0(ptr %a)
  79   ret %struct.uint16x4x3_t %tmp
  80 }
  81
  82 ; CHECK-LABEL: test_vld1_u16_x4
  83 ; CHECK: vld1.16 {d16, d17, d18, d19}, [r1:256]
  84 define %struct.uint16x4x4_t @test_vld1_u16_x4(ptr %a) nounwind {
  85   %tmp = tail call %struct.uint16x4x4_t @llvm.arm.neon.vld1x4.v4i16.p0(ptr %a)
  86   ret %struct.uint16x4x4_t %tmp
  87 }
  88
  89 ; CHECK-LABEL: test_vld1_u32_x2
  90 ; CHECK: vld1.32 {d16, d17}, [r0:64]
  91 define %struct.uint32x2x2_t @test_vld1_u32_x2(ptr %a) nounwind {
  92   %tmp = tail call %struct.uint32x2x2_t @llvm.arm.neon.vld1x2.v2i32.p0(ptr %a)
  93   ret %struct.uint32x2x2_t %tmp
  94 }
  95
  96 ; CHECK-LABEL: test_vld1_u32_x3
  97 ; CHECK: vld1.32 {d16, d17, d18}, [r1:64]
  98 define %struct.uint32x2x3_t @test_vld1_u32_x3(ptr %a) nounwind {
  99   %tmp = tail call %struct.uint32x2x3_t @llvm.arm.neon.vld1x3.v2i32.p0(ptr %a)
 100   ret %struct.uint32x2x3_t %tmp
 101 }
 102
 103 ; CHECK-LABEL: test_vld1_u32_x4
 104 ; CHECK: vld1.32 {d16, d17, d18, d19}, [r1:256]
 105 define %struct.uint32x2x4_t @test_vld1_u32_x4(ptr %a) nounwind {
 106   %tmp = tail call %struct.uint32x2x4_t @llvm.arm.neon.vld1x4.v2i32.p0(ptr %a)
 107   ret %struct.uint32x2x4_t %tmp
 108 }
 109
 110 ; CHECK-LABEL: test_vld1_u64_x2
 111 ; CHECK: vld1.64 {d16, d17}, [r0:64]
 112 define %struct.uint64x1x2_t @test_vld1_u64_x2(ptr %a) nounwind {
 113   %tmp = tail call %struct.uint64x1x2_t @llvm.arm.neon.vld1x2.v1i64.p0(ptr %a)
 114   ret %struct.uint64x1x2_t %tmp
 115 }
 116
 117 ; CHECK-LABEL: test_vld1_u64_x3
 118 ; CHECK: vld1.64 {d16, d17, d18}, [r1:64]
 119 define %struct.uint64x1x3_t @test_vld1_u64_x3(ptr %a) nounwind {
 120   %tmp = tail call %struct.uint64x1x3_t @llvm.arm.neon.vld1x3.v1i64.p0(ptr %a)
 121   ret %struct.uint64x1x3_t %tmp
 122 }
 123
 124 ; CHECK-LABEL: test_vld1_u64_x4
 125 ; CHECK: vld1.64 {d16, d17, d18, d19}, [r1:256]
 126 define %struct.uint64x1x4_t @test_vld1_u64_x4(ptr %a) nounwind {
 127   %tmp = tail call %struct.uint64x1x4_t @llvm.arm.neon.vld1x4.v1i64.p0(ptr %a)
 128   ret %struct.uint64x1x4_t %tmp
 129 }
 130
 131 ; CHECK-LABEL: test_vld1_u8_x2
 132 ; CHECK: vld1.8 {d16, d17}, [r0:64]
 133 define %struct.uint8x8x2_t @test_vld1_u8_x2(ptr %a) nounwind {
 134   %tmp = tail call %struct.uint8x8x2_t @llvm.arm.neon.vld1x2.v8i8.p0(ptr %a)
 135   ret %struct.uint8x8x2_t %tmp
 136 }
 137
 138 ; CHECK-LABEL: test_vld1_u8_x3
 139 ; CHECK: vld1.8 {d16, d17, d18}, [r1:64]
 140 define %struct.uint8x8x3_t @test_vld1_u8_x3(ptr %a) nounwind {
 141   %tmp = tail call %struct.uint8x8x3_t @llvm.arm.neon.vld1x3.v8i8.p0(ptr %a)
 142   ret %struct.uint8x8x3_t %tmp
 143 }
 144
 145 ; CHECK-LABEL: test_vld1_u8_x4
 146 ; CHECK: vld1.8 {d16, d17, d18, d19}, [r1:256]
 147 define %struct.uint8x8x4_t @test_vld1_u8_x4(ptr %a) nounwind {
 148   %tmp = tail call %struct.uint8x8x4_t @llvm.arm.neon.vld1x4.v8i8.p0(ptr %a)
 149   ret %struct.uint8x8x4_t %tmp
 150 }
 151
 152 ; CHECK-LABEL: test_vld1q_u16_x2
 153 ; CHECK: vld1.16 {d16, d17, d18, d19}, [r1:256]
 154 define %struct.uint16x8x2_t @test_vld1q_u16_x2(ptr %a) nounwind {
 155   %tmp = tail call %struct.uint16x8x2_t @llvm.arm.neon.vld1x2.v8i16.p0(ptr %a)
 156   ret %struct.uint16x8x2_t %tmp
 157 }
 158
 159 ; CHECK-LABEL: test_vld1q_u16_x3
 160 ; CHECK: vld1.16 {d16, d17, d18}, [r1:64]!
 161 ; CHECK: vld1.16 {d19, d20, d21}, [r1:64]
 162 define %struct.uint16x8x3_t @test_vld1q_u16_x3(ptr %a) nounwind {
 163   %tmp = tail call %struct.uint16x8x3_t @llvm.arm.neon.vld1x3.v8i16.p0(ptr %a)
 164   ret %struct.uint16x8x3_t %tmp
 165 }
 166
 167 ; CHECK-LABEL: test_vld1q_u16_x4
 168 ; CHECK: vld1.16 {d16, d17, d18, d19}, [r1:256]!
 169 ; CHECK: vld1.16 {d20, d21, d22, d23}, [r1:256]
 170 define %struct.uint16x8x4_t @test_vld1q_u16_x4(ptr %a) nounwind {
 171   %tmp = tail call %struct.uint16x8x4_t @llvm.arm.neon.vld1x4.v8i16.p0(ptr %a)
 172   ret %struct.uint16x8x4_t %tmp
 173 }
 174
 175 ; CHECK-LABEL: test_vld1q_u32_x2
 176 ; CHECK: vld1.32 {d16, d17, d18, d19}, [r1:256]
 177 define %struct.uint32x4x2_t @test_vld1q_u32_x2(ptr %a) nounwind {
 178   %tmp = tail call %struct.uint32x4x2_t @llvm.arm.neon.vld1x2.v4i32.p0(ptr %a)
 179   ret %struct.uint32x4x2_t %tmp
 180 }
 181
 182 ; CHECK-LABEL: test_vld1q_u32_x3
 183 ; CHECK: vld1.32 {d16, d17, d18}, [r1:64]!
 184 ; CHECK: vld1.32 {d19, d20, d21}, [r1:64]
 185 define %struct.uint32x4x3_t @test_vld1q_u32_x3(ptr %a) nounwind {
 186   %tmp = tail call %struct.uint32x4x3_t @llvm.arm.neon.vld1x3.v4i32.p0(ptr %a)
 187   ret %struct.uint32x4x3_t %tmp
 188 }
 189
 190 ; CHECK-LABEL: test_vld1q_u32_x4
 191 ; CHECK: vld1.32 {d16, d17, d18, d19}, [r1:256]!
 192 ; CHECK: vld1.32 {d20, d21, d22, d23}, [r1:256]
 193 define %struct.uint32x4x4_t @test_vld1q_u32_x4(ptr %a) nounwind {
 194   %tmp = tail call %struct.uint32x4x4_t @llvm.arm.neon.vld1x4.v4i32.p0(ptr %a)
 195   ret %struct.uint32x4x4_t %tmp
 196 }
 197
 198 ; CHECK-LABEL: test_vld1q_u64_x2
 199 ; CHECK: vld1.64 {d16, d17, d18, d19}, [r1:256]
 200 define %struct.uint64x2x2_t @test_vld1q_u64_x2(ptr %a) nounwind {
 201   %tmp = tail call %struct.uint64x2x2_t @llvm.arm.neon.vld1x2.v2i64.p0(ptr %a)
 202   ret %struct.uint64x2x2_t %tmp
 203 }
 204
 205 ; CHECK-LABEL: test_vld1q_u64_x3
 206 ; CHECK: vld1.64 {d16, d17, d18}, [r1:64]!
 207 ; CHECK: vld1.64 {d19, d20, d21}, [r1:64]
 208 define %struct.uint64x2x3_t @test_vld1q_u64_x3(ptr %a) nounwind {
 209   %tmp = tail call %struct.uint64x2x3_t @llvm.arm.neon.vld1x3.v2i64.p0(ptr %a)
 210   ret %struct.uint64x2x3_t %tmp
 211 }
 212
 213 ; CHECK-LABEL: test_vld1q_u64_x4
 214 ; CHECK: vld1.64 {d16, d17, d18, d19}, [r1:256]!
 215 ; CHECK: vld1.64 {d20, d21, d22, d23}, [r1:256]
 216 define %struct.uint64x2x4_t @test_vld1q_u64_x4(ptr %a) nounwind {
 217   %tmp = tail call %struct.uint64x2x4_t @llvm.arm.neon.vld1x4.v2i64.p0(ptr %a)
 218   ret %struct.uint64x2x4_t %tmp
 219 }
 220
 221 ; CHECK-LABEL: test_vld1q_u8_x2
 222 ; CHECK: vld1.8 {d16, d17, d18, d19}, [r1:256]
 223 define %struct.uint8x16x2_t @test_vld1q_u8_x2(ptr %a) nounwind {
 224   %tmp = tail call %struct.uint8x16x2_t @llvm.arm.neon.vld1x2.v16i8.p0(ptr %a)
 225   ret %struct.uint8x16x2_t %tmp
 226 }
 227
 228 ; CHECK-LABEL: test_vld1q_u8_x3
 229 ; CHECK: vld1.8 {d16, d17, d18}, [r1:64]!
 230 ; CHECK: vld1.8 {d19, d20, d21}, [r1:64]
 231 define %struct.uint8x16x3_t @test_vld1q_u8_x3(ptr %a) nounwind {
 232   %tmp = tail call %struct.uint8x16x3_t @llvm.arm.neon.vld1x3.v16i8.p0(ptr %a)
 233   ret %struct.uint8x16x3_t %tmp
 234 }
 235
 236 ; CHECK-LABEL: test_vld1q_u8_x4
 237 ; CHECK: vld1.8 {d16, d17, d18, d19}, [r1:256]!
 238 ; CHECK: vld1.8 {d20, d21, d22, d23}, [r1:256]
 239 define %struct.uint8x16x4_t @test_vld1q_u8_x4(ptr %a) nounwind {
 240   %tmp = tail call %struct.uint8x16x4_t @llvm.arm.neon.vld1x4.v16i8.p0(ptr %a)
 241   ret %struct.uint8x16x4_t %tmp
 242 }
 243
 244 ; Post-increment.
 245
 246 define %struct.uint16x4x2_t @test_vld1_u16_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 247 ; CHECK-LABEL: test_vld1_u16_x2_post_imm:
 248 ; CHECK:         vld1.16 {d16, d17}, [r0:64]!
 249   %ld = tail call %struct.uint16x4x2_t @llvm.arm.neon.vld1x2.v4i16.p0(ptr %a)
 250   %tmp = getelementptr i16, ptr %a, i32 8
 251   store ptr %tmp, ptr %ptr
 252   ret %struct.uint16x4x2_t %ld
 253 }
 254
 255 define %struct.uint16x4x2_t @test_vld1_u16_x2_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 256 ; CHECK-LABEL: test_vld1_u16_x2_post_reg:
 257 ; CHECK:         lsl r2, r2, #1
 258 ; CHECK-NEXT:    vld1.16 {d16, d17}, [r0:64], r2
 259   %ld = tail call %struct.uint16x4x2_t @llvm.arm.neon.vld1x2.v4i16.p0(ptr %a)
 260   %tmp = getelementptr i16, ptr %a, i32 %inc
 261   store ptr %tmp, ptr %ptr
 262   ret %struct.uint16x4x2_t %ld
 263 }
 264
 265 define %struct.uint16x4x3_t @test_vld1_u16_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 266 ; CHECK-LABEL: test_vld1_u16_x3_post_imm:
 267 ; CHECK:         vld1.16 {d16, d17, d18}, [r1:64]!
 268   %ld = tail call %struct.uint16x4x3_t @llvm.arm.neon.vld1x3.v4i16.p0(ptr %a)
 269   %tmp = getelementptr i16, ptr %a, i32 12
 270   store ptr %tmp, ptr %ptr
 271   ret %struct.uint16x4x3_t %ld
 272 }
 273
 274 define %struct.uint16x4x3_t @test_vld1_u16_x3_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 275 ; CHECK-LABEL: test_vld1_u16_x3_post_reg:
 276 ; CHECK:         lsl r3, r3, #1
 277 ; CHECK-NEXT:    vld1.16 {d16, d17, d18}, [r1:64], r3
 278   %ld = tail call %struct.uint16x4x3_t @llvm.arm.neon.vld1x3.v4i16.p0(ptr %a)
 279   %tmp = getelementptr i16, ptr %a, i32 %inc
 280   store ptr %tmp, ptr %ptr
 281   ret %struct.uint16x4x3_t %ld
 282 }
 283
 284 define %struct.uint16x4x4_t @test_vld1_u16_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 285 ; CHECK-LABEL: test_vld1_u16_x4_post_imm:
 286 ; CHECK:         vld1.16 {d16, d17, d18, d19}, [r1:256]!
 287   %ld = tail call %struct.uint16x4x4_t @llvm.arm.neon.vld1x4.v4i16.p0(ptr %a)
 288   %tmp = getelementptr i16, ptr %a, i32 16
 289   store ptr %tmp, ptr %ptr
 290   ret %struct.uint16x4x4_t %ld
 291 }
 292
 293 define %struct.uint16x4x4_t @test_vld1_u16_x4_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 294 ; CHECK-LABEL: test_vld1_u16_x4_post_reg:
 295 ; CHECK:         lsl r3, r3, #1
 296 ; CHECK-NEXT:    vld1.16 {d16, d17, d18, d19}, [r1:256], r3
 297   %ld = tail call %struct.uint16x4x4_t @llvm.arm.neon.vld1x4.v4i16.p0(ptr %a)
 298   %tmp = getelementptr i16, ptr %a, i32 %inc
 299   store ptr %tmp, ptr %ptr
 300   ret %struct.uint16x4x4_t %ld
 301 }
 302
 303 define %struct.uint32x2x2_t @test_vld1_u32_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 304 ; CHECK-LABEL: test_vld1_u32_x2_post_imm:
 305 ; CHECK:         vld1.32 {d16, d17}, [r0:64]!
 306   %ld = tail call %struct.uint32x2x2_t @llvm.arm.neon.vld1x2.v2i32.p0(ptr %a)
 307   %tmp = getelementptr i32, ptr %a, i32 4
 308   store ptr %tmp, ptr %ptr
 309   ret %struct.uint32x2x2_t %ld
 310 }
 311
 312 define %struct.uint32x2x2_t @test_vld1_u32_x2_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 313 ; CHECK-LABEL: test_vld1_u32_x2_post_reg:
 314 ; CHECK:         lsl r2, r2, #2
 315 ; CHECK-NEXT:    vld1.32 {d16, d17}, [r0:64], r2
 316   %ld = tail call %struct.uint32x2x2_t @llvm.arm.neon.vld1x2.v2i32.p0(ptr %a)
 317   %tmp = getelementptr i32, ptr %a, i32 %inc
 318   store ptr %tmp, ptr %ptr
 319   ret %struct.uint32x2x2_t %ld
 320 }
 321
 322 define %struct.uint32x2x3_t @test_vld1_u32_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 323 ; CHECK-LABEL: test_vld1_u32_x3_post_imm:
 324 ; CHECK:         vld1.32 {d16, d17, d18}, [r1:64]!
 325   %ld = tail call %struct.uint32x2x3_t @llvm.arm.neon.vld1x3.v2i32.p0(ptr %a)
 326   %tmp = getelementptr i32, ptr %a, i32 6
 327   store ptr %tmp, ptr %ptr
 328   ret %struct.uint32x2x3_t %ld
 329 }
 330
 331 define %struct.uint32x2x3_t @test_vld1_u32_x3_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 332 ; CHECK-LABEL: test_vld1_u32_x3_post_reg:
 333 ; CHECK:         lsl r3, r3, #2
 334 ; CHECK-NEXT:    vld1.32 {d16, d17, d18}, [r1:64], r3
 335   %ld = tail call %struct.uint32x2x3_t @llvm.arm.neon.vld1x3.v2i32.p0(ptr %a)
 336   %tmp = getelementptr i32, ptr %a, i32 %inc
 337   store ptr %tmp, ptr %ptr
 338   ret %struct.uint32x2x3_t %ld
 339 }
 340
 341 define %struct.uint32x2x4_t @test_vld1_u32_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 342 ; CHECK-LABEL: test_vld1_u32_x4_post_imm:
 343 ; CHECK:         vld1.32 {d16, d17, d18, d19}, [r1:256]!
 344   %ld = tail call %struct.uint32x2x4_t @llvm.arm.neon.vld1x4.v2i32.p0(ptr %a)
 345   %tmp = getelementptr i32, ptr %a, i32 8
 346   store ptr %tmp, ptr %ptr
 347   ret %struct.uint32x2x4_t %ld
 348 }
 349
 350 define %struct.uint32x2x4_t @test_vld1_u32_x4_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 351 ; CHECK-LABEL: test_vld1_u32_x4_post_reg:
 352 ; CHECK:         lsl r3, r3, #2
 353 ; CHECK-NEXT:    vld1.32 {d16, d17, d18, d19}, [r1:256], r3
 354   %ld = tail call %struct.uint32x2x4_t @llvm.arm.neon.vld1x4.v2i32.p0(ptr %a)
 355   %tmp = getelementptr i32, ptr %a, i32 %inc
 356   store ptr %tmp, ptr %ptr
 357   ret %struct.uint32x2x4_t %ld
 358 }
 359
 360 define %struct.uint64x1x2_t @test_vld1_u64_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 361 ; CHECK-LABEL: test_vld1_u64_x2_post_imm:
 362 ; CHECK:         vld1.64 {d16, d17}, [r0:64]!
 363   %ld = tail call %struct.uint64x1x2_t @llvm.arm.neon.vld1x2.v1i64.p0(ptr %a)
 364   %tmp = getelementptr i64, ptr %a, i32 2
 365   store ptr %tmp, ptr %ptr
 366   ret %struct.uint64x1x2_t %ld
 367 }
 368
 369 define %struct.uint64x1x2_t @test_vld1_u64_x2_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 370 ; CHECK-LABEL: test_vld1_u64_x2_post_reg:
 371 ; CHECK:         lsl r2, r2, #3
 372 ; CHECK-NEXT:    vld1.64 {d16, d17}, [r0:64], r2
 373   %ld = tail call %struct.uint64x1x2_t @llvm.arm.neon.vld1x2.v1i64.p0(ptr %a)
 374   %tmp = getelementptr i64, ptr %a, i32 %inc
 375   store ptr %tmp, ptr %ptr
 376   ret %struct.uint64x1x2_t %ld
 377 }
 378
 379 define %struct.uint64x1x3_t @test_vld1_u64_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 380 ; CHECK-LABEL: test_vld1_u64_x3_post_imm:
 381 ; CHECK:         vld1.64 {d16, d17, d18}, [r1:64]!
 382   %ld = tail call %struct.uint64x1x3_t @llvm.arm.neon.vld1x3.v1i64.p0(ptr %a)
 383   %tmp = getelementptr i64, ptr %a, i32 3
 384   store ptr %tmp, ptr %ptr
 385   ret %struct.uint64x1x3_t %ld
 386 }
 387
 388 define %struct.uint64x1x3_t @test_vld1_u64_x3_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 389 ; CHECK-LABEL: test_vld1_u64_x3_post_reg:
 390 ; CHECK:         lsl r3, r3, #3
 391 ; CHECK-NEXT:    vld1.64 {d16, d17, d18}, [r1:64], r3
 392   %ld = tail call %struct.uint64x1x3_t @llvm.arm.neon.vld1x3.v1i64.p0(ptr %a)
 393   %tmp = getelementptr i64, ptr %a, i32 %inc
 394   store ptr %tmp, ptr %ptr
 395   ret %struct.uint64x1x3_t %ld
 396 }
 397
 398 define %struct.uint64x1x4_t @test_vld1_u64_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 399 ; CHECK-LABEL: test_vld1_u64_x4_post_imm:
 400 ; CHECK:         vld1.64 {d16, d17, d18, d19}, [r1:256]!
 401   %ld = tail call %struct.uint64x1x4_t @llvm.arm.neon.vld1x4.v1i64.p0(ptr %a)
 402   %tmp = getelementptr i64, ptr %a, i32 4
 403   store ptr %tmp, ptr %ptr
 404   ret %struct.uint64x1x4_t %ld
 405 }
 406
 407 define %struct.uint64x1x4_t @test_vld1_u64_x4_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 408 ; CHECK-LABEL: test_vld1_u64_x4_post_reg:
 409 ; CHECK:         lsl r3, r3, #3
 410 ; CHECK-NEXT:    vld1.64 {d16, d17, d18, d19}, [r1:256], r3
 411   %ld = tail call %struct.uint64x1x4_t @llvm.arm.neon.vld1x4.v1i64.p0(ptr %a)
 412   %tmp = getelementptr i64, ptr %a, i32 %inc
 413   store ptr %tmp, ptr %ptr
 414   ret %struct.uint64x1x4_t %ld
 415 }
 416
 417 define %struct.uint8x8x2_t @test_vld1_u8_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 418 ; CHECK-LABEL: test_vld1_u8_x2_post_imm:
 419 ; CHECK:         vld1.8 {d16, d17}, [r0:64]!
 420   %ld = tail call %struct.uint8x8x2_t @llvm.arm.neon.vld1x2.v8i8.p0(ptr %a)
 421   %tmp = getelementptr i8, ptr %a, i32 16
 422   store ptr %tmp, ptr %ptr
 423   ret %struct.uint8x8x2_t %ld
 424 }
 425
 426 define %struct.uint8x8x2_t @test_vld1_u8_x2_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 427 ; CHECK-LABEL: test_vld1_u8_x2_post_reg:
 428 ; CHECK:         vld1.8 {d16, d17}, [r0:64], r2
 429   %ld = tail call %struct.uint8x8x2_t @llvm.arm.neon.vld1x2.v8i8.p0(ptr %a)
 430   %tmp = getelementptr i8, ptr %a, i32 %inc
 431   store ptr %tmp, ptr %ptr
 432   ret %struct.uint8x8x2_t %ld
 433 }
 434
 435 define %struct.uint8x8x3_t @test_vld1_u8_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 436 ; CHECK-LABEL: test_vld1_u8_x3_post_imm:
 437 ; CHECK:         vld1.8 {d16, d17, d18}, [r1:64]!
 438   %ld = tail call %struct.uint8x8x3_t @llvm.arm.neon.vld1x3.v8i8.p0(ptr %a)
 439   %tmp = getelementptr i8, ptr %a, i32 24
 440   store ptr %tmp, ptr %ptr
 441   ret %struct.uint8x8x3_t %ld
 442 }
 443
 444 define %struct.uint8x8x3_t @test_vld1_u8_x3_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 445 ; CHECK-LABEL: test_vld1_u8_x3_post_reg:
 446 ; CHECK:         vld1.8 {d16, d17, d18}, [r1:64], r3
 447   %ld = tail call %struct.uint8x8x3_t @llvm.arm.neon.vld1x3.v8i8.p0(ptr %a)
 448   %tmp = getelementptr i8, ptr %a, i32 %inc
 449   store ptr %tmp, ptr %ptr
 450   ret %struct.uint8x8x3_t %ld
 451 }
 452
 453 define %struct.uint8x8x4_t @test_vld1_u8_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 454 ; CHECK-LABEL: test_vld1_u8_x4_post_imm:
 455 ; CHECK:         vld1.8 {d16, d17, d18, d19}, [r1:256]!
 456   %ld = tail call %struct.uint8x8x4_t @llvm.arm.neon.vld1x4.v8i8.p0(ptr %a)
 457   %tmp = getelementptr i8, ptr %a, i32 32
 458   store ptr %tmp, ptr %ptr
 459   ret %struct.uint8x8x4_t %ld
 460 }
 461
 462 define %struct.uint8x8x4_t @test_vld1_u8_x4_post_reg(ptr %a, ptr %ptr, i32 %inc) nounwind {
 463 ; CHECK-LABEL: test_vld1_u8_x4_post_reg:
 464 ; CHECK:         vld1.8 {d16, d17, d18, d19}, [r1:256], r3
 465   %ld = tail call %struct.uint8x8x4_t @llvm.arm.neon.vld1x4.v8i8.p0(ptr %a)
 466   %tmp = getelementptr i8, ptr %a, i32 %inc
 467   store ptr %tmp, ptr %ptr
 468   ret %struct.uint8x8x4_t %ld
 469 }
 470
 471 define %struct.uint16x8x2_t @test_vld1q_u16_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 472 ; CHECK-LABEL: test_vld1q_u16_x2_post_imm:
 473 ; CHECK:         vld1.16 {d16, d17, d18, d19}, [r1:256]!
 474   %ld = tail call %struct.uint16x8x2_t @llvm.arm.neon.vld1x2.v8i16.p0(ptr %a)
 475   %tmp = getelementptr i16, ptr %a, i32 16
 476   store ptr %tmp, ptr %ptr
 477   ret %struct.uint16x8x2_t %ld
 478 }
 479
 480 define %struct.uint16x8x3_t @test_vld1q_u16_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 481 ; CHECK-LABEL: test_vld1q_u16_x3_post_imm:
 482 ; CHECK:         vld1.16 {d16, d17, d18}, [r1:64]!
 483 ; CHECK-NEXT:    vld1.16 {d19, d20, d21}, [r1:64]!
 484   %ld = tail call %struct.uint16x8x3_t @llvm.arm.neon.vld1x3.v8i16.p0(ptr %a)
 485   %tmp = getelementptr i16, ptr %a, i32 24
 486   store ptr %tmp, ptr %ptr
 487   ret %struct.uint16x8x3_t %ld
 488 }
 489
 490 define %struct.uint16x8x4_t @test_vld1q_u16_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 491 ; CHECK-LABEL: test_vld1q_u16_x4_post_imm:
 492 ; CHECK:         vld1.16 {d16, d17, d18, d19}, [r1:256]!
 493 ; CHECK-NEXT:    vld1.16 {d20, d21, d22, d23}, [r1:256]!
 494   %ld = tail call %struct.uint16x8x4_t @llvm.arm.neon.vld1x4.v8i16.p0(ptr %a)
 495   %tmp = getelementptr i16, ptr %a, i32 32
 496   store ptr %tmp, ptr %ptr
 497   ret %struct.uint16x8x4_t %ld
 498 }
 499
 500 define %struct.uint32x4x2_t @test_vld1q_u32_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 501 ; CHECK-LABEL: test_vld1q_u32_x2_post_imm:
 502 ; CHECK:         vld1.32 {d16, d17, d18, d19}, [r1:256]!
 503   %ld = tail call %struct.uint32x4x2_t @llvm.arm.neon.vld1x2.v4i32.p0(ptr %a)
 504   %tmp = getelementptr i32, ptr %a, i32 8
 505   store ptr %tmp, ptr %ptr
 506   ret %struct.uint32x4x2_t %ld
 507 }
 508
 509 define %struct.uint32x4x3_t @test_vld1q_u32_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 510 ; CHECK-LABEL: test_vld1q_u32_x3_post_imm:
 511 ; CHECK:         vld1.32 {d16, d17, d18}, [r1:64]!
 512 ; CHECK-NEXT:    vld1.32 {d19, d20, d21}, [r1:64]!
 513   %ld = tail call %struct.uint32x4x3_t @llvm.arm.neon.vld1x3.v4i32.p0(ptr %a)
 514   %tmp = getelementptr i32, ptr %a, i32 12
 515   store ptr %tmp, ptr %ptr
 516   ret %struct.uint32x4x3_t %ld
 517 }
 518
 519 define %struct.uint32x4x4_t @test_vld1q_u32_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 520 ; CHECK-LABEL: test_vld1q_u32_x4_post_imm:
 521 ; CHECK:         vld1.32 {d16, d17, d18, d19}, [r1:256]!
 522 ; CHECK-NEXT:    vld1.32 {d20, d21, d22, d23}, [r1:256]!
 523   %ld = tail call %struct.uint32x4x4_t @llvm.arm.neon.vld1x4.v4i32.p0(ptr %a)
 524   %tmp = getelementptr i32, ptr %a, i32 16
 525   store ptr %tmp, ptr %ptr
 526   ret %struct.uint32x4x4_t %ld
 527 }
 528
 529 define %struct.uint64x2x2_t @test_vld1q_u64_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 530 ; CHECK-LABEL: test_vld1q_u64_x2_post_imm:
 531 ; CHECK:         vld1.64 {d16, d17, d18, d19}, [r1:256]!
 532   %ld = tail call %struct.uint64x2x2_t @llvm.arm.neon.vld1x2.v2i64.p0(ptr %a)
 533   %tmp = getelementptr i64, ptr %a, i32 4
 534   store ptr %tmp, ptr %ptr
 535   ret %struct.uint64x2x2_t %ld
 536 }
 537
 538 define %struct.uint64x2x3_t @test_vld1q_u64_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 539 ; CHECK-LABEL: test_vld1q_u64_x3_post_imm:
 540 ; CHECK:         vld1.64 {d16, d17, d18}, [r1:64]!
 541 ; CHECK-NEXT:    vld1.64 {d19, d20, d21}, [r1:64]!
 542   %ld = tail call %struct.uint64x2x3_t @llvm.arm.neon.vld1x3.v2i64.p0(ptr %a)
 543   %tmp = getelementptr i64, ptr %a, i32 6
 544   store ptr %tmp, ptr %ptr
 545   ret %struct.uint64x2x3_t %ld
 546 }
 547
 548 define %struct.uint64x2x4_t @test_vld1q_u64_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 549 ; CHECK-LABEL: test_vld1q_u64_x4_post_imm:
 550 ; CHECK:         vld1.64 {d16, d17, d18, d19}, [r1:256]!
 551 ; CHECK-NEXT:    vld1.64 {d20, d21, d22, d23}, [r1:256]!
 552   %ld = tail call %struct.uint64x2x4_t @llvm.arm.neon.vld1x4.v2i64.p0(ptr %a)
 553   %tmp = getelementptr i64, ptr %a, i32 8
 554   store ptr %tmp, ptr %ptr
 555   ret %struct.uint64x2x4_t %ld
 556 }
 557
 558 define %struct.uint8x16x2_t @test_vld1q_u8_x2_post_imm(ptr %a, ptr %ptr) nounwind {
 559 ; CHECK-LABEL: test_vld1q_u8_x2_post_imm:
 560 ; CHECK:         vld1.8 {d16, d17, d18, d19}, [r1:256]!
 561   %ld = tail call %struct.uint8x16x2_t @llvm.arm.neon.vld1x2.v16i8.p0(ptr %a)
 562   %tmp = getelementptr i8, ptr %a, i32 32
 563   store ptr %tmp, ptr %ptr
 564   ret %struct.uint8x16x2_t %ld
 565 }
 566
 567 define %struct.uint8x16x3_t @test_vld1q_u8_x3_post_imm(ptr %a, ptr %ptr) nounwind {
 568 ; CHECK-LABEL: test_vld1q_u8_x3_post_imm:
 569 ; CHECK:         vld1.8 {d16, d17, d18}, [r1:64]!
 570 ; CHECK-NEXT:    vld1.8 {d19, d20, d21}, [r1:64]!
 571   %ld = tail call %struct.uint8x16x3_t @llvm.arm.neon.vld1x3.v16i8.p0(ptr %a)
 572   %tmp = getelementptr i8, ptr %a, i32 48
 573   store ptr %tmp, ptr %ptr
 574   ret %struct.uint8x16x3_t %ld
 575 }
 576
 577 define %struct.uint8x16x4_t @test_vld1q_u8_x4_post_imm(ptr %a, ptr %ptr) nounwind {
 578 ; CHECK-LABEL: test_vld1q_u8_x4_post_imm:
 579 ; CHECK:         vld1.8 {d16, d17, d18, d19}, [r1:256]!
 580 ; CHECK-NEXT:    vld1.8 {d20, d21, d22, d23}, [r1:256]!
 581   %ld = tail call %struct.uint8x16x4_t @llvm.arm.neon.vld1x4.v16i8.p0(ptr %a)
 582   %tmp = getelementptr i8, ptr %a, i32 64
 583   store ptr %tmp, ptr %ptr
 584   ret %struct.uint8x16x4_t %ld
 585 }