arm64-lanes.c revision 6bcf27bb9a4b5c3f79cb44c0e4654a6d7619ad89
16bcf27bb9a4b5c3f79cb44c0e4654a6d7619ad89Stephen Hines// RUN: %clang_cc1 -O3 -triple arm64-apple-ios7 -target-feature +neon -ffreestanding -emit-llvm -o - %s | FileCheck %s 2651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 3651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines#include <arm_neon.h> 4651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 5651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdupb_lane_s8 6651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesint8_t test_vdupb_lane_s8(int8x8_t src) { 7651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdupb_lane_s8(src, 2); 8651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <8 x i8> %src, i32 2 9651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 10651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 11651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdupb_lane_u8 12651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesuint8_t test_vdupb_lane_u8(uint8x8_t src) { 13651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdupb_lane_u8(src, 2); 14651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <8 x i8> %src, i32 2 15651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 16651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 17651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vduph_lane_s16 18651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesint16_t test_vduph_lane_s16(int16x4_t src) { 19651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vduph_lane_s16(src, 2); 20651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <4 x i16> %src, i32 2 21651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 22651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 23651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vduph_lane_u16 24651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesuint16_t test_vduph_lane_u16(uint16x4_t src) { 25651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vduph_lane_u16(src, 2); 26651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <4 x i16> %src, i32 2 27651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 28651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 29651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdups_lane_s32 30651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesint32_t test_vdups_lane_s32(int32x2_t src) { 31651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdups_lane_s32(src, 0); 32651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <2 x i32> %src, i32 0 33651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 34651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 35651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdups_lane_u32 36651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesuint32_t test_vdups_lane_u32(uint32x2_t src) { 37651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdups_lane_u32(src, 0); 38651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <2 x i32> %src, i32 0 39651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 40651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 41651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdups_lane_f32 42651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat32_t test_vdups_lane_f32(float32x2_t src) { 43651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdups_lane_f32(src, 0); 44651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <2 x float> %src, i32 0 45651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 46651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 47651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdupd_lane_s64 48651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesint64_t test_vdupd_lane_s64(int64x1_t src) { 49651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdupd_lane_s64(src, 0); 50651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <1 x i64> %src, i32 0 51651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 52651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 53651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdupd_lane_u64 54651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesuint64_t test_vdupd_lane_u64(uint64x1_t src) { 55651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdupd_lane_u64(src, 0); 56651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <1 x i64> %src, i32 0 57651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 58651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines 59651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines// CHECK-LABEL: @test_vdupd_lane_f64 60651f13cea278ec967336033dd032faef0e9fc2ecStephen Hinesfloat64_t test_vdupd_lane_f64(float64x1_t src) { 61651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines return vdupd_lane_f64(src, 0); 62651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines // CHECK: extractelement <1 x double> %src, i32 0 63651f13cea278ec967336033dd032faef0e9fc2ecStephen Hines} 64