1f79470583759d20c20268711e6111461aefa8461Jim Grosbach// REQUIRES: arm-registered-target 297fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: %clang_cc1 -triple thumbv7-apple-darwin \ 397fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: -target-abi apcs-gnu \ 497fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: -target-cpu cortex-a8 \ 597fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: -mfloat-abi soft \ 697fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: -target-feature +soft-float-abi \ 797fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: -ffreestanding \ 897fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// RUN: -emit-llvm -w -o - %s | FileCheck %s 997fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson 1097fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson#include <arm_neon.h> 1197fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson 1297fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// Radar 9311427: Check that alignment specifier is used in Neon load/store 1397fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson// intrinsics. 1497fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilsontypedef float AlignedAddr __attribute__ ((aligned (16))); 1597fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilsonvoid t1(AlignedAddr *addr1, AlignedAddr *addr2) { 16eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson// CHECK: @t1 1787d948ecccffea9e9e37d0d053b246e2d6d6c47bPirama Arumuga Nainar// CHECK: call <4 x float> @llvm.arm.neon.vld1.v4f32.p0i8(i8* %{{.*}}, i32 16) 1897fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson float32x4_t a = vld1q_f32(addr1); 1987d948ecccffea9e9e37d0d053b246e2d6d6c47bPirama Arumuga Nainar// CHECK: call void @llvm.arm.neon.vst1.p0i8.v4f32(i8* %{{.*}}, <4 x float> %{{.*}}, i32 16) 2097fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson vst1q_f32(addr2, a); 2197fb6f33f7ff850c2ce8a52e1f2ad9eb520d71e0Bob Wilson} 22eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson 23eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson// Radar 10538555: Make sure unaligned load/stores do not gain alignment. 24eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilsonvoid t2(char *addr) { 25eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson// CHECK: @t2 263ea9e33ea25e0c2b12db56418ba3f994eb662c04Pirama Arumuga Nainar// CHECK: load i32, i32* %{{.*}}, align 1 27eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson int32x2_t vec = vld1_dup_s32(addr); 28eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson// CHECK: store i32 %{{.*}}, i32* {{.*}}, align 1 29eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson vst1_lane_s32(addr, vec, 1); 30eac1f6746a2915fea3ed42284b07e274c0095a95Bob Wilson} 31