1 // RUN: %clang_cc1 -triple arm64-apple-ios7 -target-feature +neon -ffreestanding -S -o - -emit-llvm %s | FileCheck %s 2 3 // Test ARM64 extract intrinsics 4 // can use as back end test by adding a run line with 5 // -check-prefix=CHECK-CODEGEN on the FileCheck 6 7 #include <arm_neon.h> 8 9 void test_vext_s8() 10 { 11 // CHECK: test_vext_s8 12 int8x8_t xS8x8; 13 xS8x8 = vext_s8(xS8x8, xS8x8, 1); 14 // CHECK: shufflevector 15 // CHECK-CODEGEN: test_vext_s8: 16 // CHECK-CODEGEN: {{ext.8.*#1}} 17 } 18 19 void test_vext_u8() 20 { 21 // CHECK: test_vext_u8 22 uint8x8_t xU8x8; 23 xU8x8 = vext_u8(xU8x8, xU8x8, 2); 24 // CHECK: shufflevector 25 // CHECK-CODEGEN: test_vext_u8: 26 // CHECK-CODEGEN: {{ext.8.*#2}} 27 } 28 29 void test_vext_p8() 30 { 31 // CHECK: test_vext_p8 32 poly8x8_t xP8x8; 33 xP8x8 = vext_p8(xP8x8, xP8x8, 3); 34 // CHECK: shufflevector 35 // CHECK-CODEGEN: test_vext_p8: 36 // CHECK-CODEGEN: {{ext.8.*#3}} 37 } 38 39 void test_vext_s16() 40 { 41 // CHECK: test_vext_s16 42 int16x4_t xS16x4; 43 xS16x4 = vext_s16(xS16x4, xS16x4, 1); 44 // CHECK: shufflevector 45 // CHECK-CODEGEN: test_vext_s16: 46 // CHECK-CODEGEN: {{ext.8.*#2}} 47 } 48 49 void test_vext_u16() 50 { 51 // CHECK: test_vext_u16 52 uint16x4_t xU16x4; 53 xU16x4 = vext_u16(xU16x4, xU16x4, 2); 54 // CHECK: shufflevector 55 // CHECK-CODEGEN: test_vext_u16: 56 // CHECK-CODEGEN: {{ext.8.*#4}} 57 } 58 59 void test_vext_p16() 60 { 61 // CHECK: test_vext_p16 62 poly16x4_t xP16x4; 63 xP16x4 = vext_p16(xP16x4, xP16x4, 3); 64 // CHECK: shufflevector 65 // CHECK-CODEGEN: test_vext_p16: 66 // CHECK-CODEGEN: {{ext.8.*#6}} 67 } 68 69 void test_vext_s32() 70 { 71 // CHECK: test_vext_s32 72 int32x2_t xS32x2; 73 xS32x2 = vext_s32(xS32x2, xS32x2, 1); 74 // CHECK: shufflevector 75 // CHECK-CODEGEN: test_vext_s32: 76 // CHECK-CODEGEN: {{ext.8.*#4}} 77 } 78 79 void test_vext_u32() 80 { 81 // CHECK: test_vext_u32 82 uint32x2_t xU32x2; 83 xU32x2 = vext_u32(xU32x2, xU32x2, 1); 84 // CHECK: shufflevector 85 // CHECK-CODEGEN: test_vext_u32: 86 // CHECK-CODEGEN: {{ext.8.*#4}} 87 } 88 89 void test_vext_f32() 90 { 91 // CHECK: test_vext_f32 92 float32x2_t xF32x2; 93 xF32x2 = vext_f32(xF32x2, xF32x2, 1); 94 // CHECK: shufflevector 95 // CHECK-CODEGEN: test_vext_f32: 96 // CHECK-CODEGEN: {{ext.8.*#4}} 97 } 98 99 void test_vext_s64() 100 { 101 // CHECK: test_vext_s64 102 int64x1_t xS64x1; 103 // FIXME don't use 1 as index or check for now, clang has a bug? 104 xS64x1 = vext_s64(xS64x1, xS64x1, /*1*/0); 105 // CHECK: shufflevector 106 // CHECK-CODEGEN: test_vext_s64: 107 // CHECK_FIXME: {{ext.8.*#0}} 108 } 109 110 void test_vext_u64() 111 { 112 // CHECK: test_vext_u64 113 uint64x1_t xU64x1; 114 // FIXME don't use 1 as index or check for now, clang has a bug? 115 xU64x1 = vext_u64(xU64x1, xU64x1, /*1*/0); 116 // CHECK: shufflevector 117 // CHECK-CODEGEN: test_vext_u64: 118 // CHECK_FIXME: {{ext.8.*#0}} 119 } 120 121 void test_vextq_s8() 122 { 123 // CHECK: test_vextq_s8 124 int8x16_t xS8x16; 125 xS8x16 = vextq_s8(xS8x16, xS8x16, 4); 126 // CHECK: shufflevector 127 // CHECK-CODEGEN: test_vextq_s8: 128 // CHECK-CODEGEN: {{ext.16.*#4}} 129 } 130 131 void test_vextq_u8() 132 { 133 // CHECK: test_vextq_u8 134 uint8x16_t xU8x16; 135 xU8x16 = vextq_u8(xU8x16, xU8x16, 5); 136 // CHECK: shufflevector 137 // CHECK-CODEGEN: test_vextq_u8: 138 // CHECK-CODEGEN: {{ext.16.*#5}} 139 } 140 141 void test_vextq_p8() 142 { 143 // CHECK: test_vextq_p8 144 poly8x16_t xP8x16; 145 xP8x16 = vextq_p8(xP8x16, xP8x16, 6); 146 // CHECK: shufflevector 147 // CHECK-CODEGEN: test_vextq_p8: 148 // CHECK-CODEGEN: {{ext.16.*#6}} 149 } 150 151 void test_vextq_s16() 152 { 153 // CHECK: test_vextq_s16 154 int16x8_t xS16x8; 155 xS16x8 = vextq_s16(xS16x8, xS16x8, 7); 156 // CHECK: shufflevector 157 // CHECK-CODEGEN: test_vextq_s16: 158 // CHECK-CODEGEN: {{ext.16.*#14}} 159 } 160 161 void test_vextq_u16() 162 { 163 // CHECK: test_vextq_u16 164 uint16x8_t xU16x8; 165 xU16x8 = vextq_u16(xU16x8, xU16x8, 4); 166 // CHECK: shufflevector 167 // CHECK-CODEGEN: test_vextq_u16: 168 // CHECK-CODEGEN: {{ext.16.*#8}} 169 } 170 171 void test_vextq_p16() 172 { 173 // CHECK: test_vextq_p16 174 poly16x8_t xP16x8; 175 xP16x8 = vextq_p16(xP16x8, xP16x8, 5); 176 // CHECK: shufflevector 177 // CHECK-CODEGEN: test_vextq_p16: 178 // CHECK-CODEGEN: {{ext.16.*#10}} 179 } 180 181 void test_vextq_s32() 182 { 183 // CHECK: test_vextq_s32 184 int32x4_t xS32x4; 185 xS32x4 = vextq_s32(xS32x4, xS32x4, 1); 186 // CHECK: shufflevector 187 // CHECK-CODEGEN: test_vextq_s32: 188 // CHECK-CODEGEN: {{ext.16.*#4}} 189 } 190 191 void test_vextq_u32() 192 { 193 // CHECK: test_vextq_u32 194 uint32x4_t xU32x4; 195 xU32x4 = vextq_u32(xU32x4, xU32x4, 2); 196 // CHECK: shufflevector 197 // CHECK-CODEGEN: test_vextq_u32: 198 // CHECK-CODEGEN: {{ext.16.*#8}} 199 } 200 201 void test_vextq_f32() 202 { 203 // CHECK: test_vextq_f32 204 float32x4_t xF32x4; 205 xF32x4 = vextq_f32(xF32x4, xF32x4, 3); 206 // CHECK: shufflevector 207 // CHECK-CODEGEN: test_vextq_f32: 208 // CHECK-CODEGEN: {{ext.16.*#12}} 209 } 210 211 void test_vextq_s64() 212 { 213 // CHECK: test_vextq_s64 214 int64x2_t xS64x2; 215 xS64x2 = vextq_s64(xS64x2, xS64x2, 1); 216 // CHECK: shufflevector 217 // CHECK-CODEGEN: test_vextq_s64: 218 // CHECK-CODEGEN: {{ext.16.*#8}} 219 } 220 221 void test_vextq_u64() 222 { 223 // CHECK: test_vextq_u64 224 uint64x2_t xU64x2; 225 xU64x2 = vextq_u64(xU64x2, xU64x2, 1); 226 // CHECK: shufflevector 227 // CHECK-CODEGEN: test_vextq_u64: 228 // CHECK-CODEGEN: {{ext.16.*#8}} 229 } 230 231 void test_vextq_f64() 232 { 233 // CHECK: test_vextq_f64 234 float64x2_t xF64x2; 235 xF64x2 = vextq_f64(xF64x2, xF64x2, 1); 236 // CHECK: shufflevector 237 // CHECK-CODEGEN: test_vextq_u64: 238 // CHECK-CODEGEN: {{ext.16.*#8}} 239 } 240
