Skip to content

Commit 70d4bb5

Browse files
arpilipearpilipe
committed
Update the expected masked load/store intrinsics names in tests
The mangling of their names was changed in order to support arbitrary addrspace pointers as arguments in rL274043. llvm-svn: 274044
1 parent 7ad95ec commit 70d4bb5

File tree

4 files changed

+84
-84
lines changed

4 files changed

+84
-84
lines changed

‎clang/test/CodeGen/avx512bw-builtins.c‎

Lines changed: 6 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -1376,30 +1376,30 @@ __mmask32 test_mm512_kunpackw(__mmask32 __A, __mmask32 __B) {
13761376

13771377
__m512i test_mm512_mask_loadu_epi16(__m512i __W, __mmask32 __U, void const *__P) {
13781378
// CHECK-LABEL: @test_mm512_mask_loadu_epi16
1379-
// CHECK: @llvm.masked.load.v32i16(<32 x i16>* %{{.*}}, i32 1, <32 x i1> %{{.*}}, <32 x i16> %{{.*}})
1379+
// CHECK: @llvm.masked.load.v32i16.p0v32i16(<32 x i16>* %{{.*}}, i32 1, <32 x i1> %{{.*}}, <32 x i16> %{{.*}})
13801380
return _mm512_mask_loadu_epi16(__W, __U, __P);
13811381
}
13821382

13831383
__m512i test_mm512_maskz_loadu_epi16(__mmask32 __U, void const *__P) {
13841384
// CHECK-LABEL: @test_mm512_maskz_loadu_epi16
1385-
// CHECK: @llvm.masked.load.v32i16(<32 x i16>* %{{.*}}, i32 1, <32 x i1> %{{.*}}, <32 x i16> %{{.*}})
1385+
// CHECK: @llvm.masked.load.v32i16.p0v32i16(<32 x i16>* %{{.*}}, i32 1, <32 x i1> %{{.*}}, <32 x i16> %{{.*}})
13861386
return _mm512_maskz_loadu_epi16(__U, __P);
13871387
}
13881388

13891389
__m512i test_mm512_mask_loadu_epi8(__m512i __W, __mmask64 __U, void const *__P) {
13901390
// CHECK-LABEL: @test_mm512_mask_loadu_epi8
1391-
// CHECK: @llvm.masked.load.v64i8(<64 x i8>* %{{.*}}, i32 1, <64 x i1> %{{.*}}, <64 x i8> %{{.*}})
1391+
// CHECK: @llvm.masked.load.v64i8.p0v64i8(<64 x i8>* %{{.*}}, i32 1, <64 x i1> %{{.*}}, <64 x i8> %{{.*}})
13921392
return _mm512_mask_loadu_epi8(__W, __U, __P);
13931393
}
13941394

13951395
__m512i test_mm512_maskz_loadu_epi8(__mmask64 __U, void const *__P) {
13961396
// CHECK-LABEL: @test_mm512_maskz_loadu_epi8
1397-
// CHECK: @llvm.masked.load.v64i8(<64 x i8>* %{{.*}}, i32 1, <64 x i1> %{{.*}}, <64 x i8> %{{.*}})
1397+
// CHECK: @llvm.masked.load.v64i8.p0v64i8(<64 x i8>* %{{.*}}, i32 1, <64 x i1> %{{.*}}, <64 x i8> %{{.*}})
13981398
return _mm512_maskz_loadu_epi8(__U, __P);
13991399
}
14001400
void test_mm512_mask_storeu_epi16(void *__P, __mmask32 __U, __m512i __A) {
14011401
// CHECK-LABEL: @test_mm512_mask_storeu_epi16
1402-
// CHECK: @llvm.masked.store.v32i16(<32 x i16> %{{.*}}, <32 x i16>* %{{.*}}, i32 1, <32 x i1> %{{.*}})
1402+
// CHECK: @llvm.masked.store.v32i16.p0v32i16(<32 x i16> %{{.*}}, <32 x i16>* %{{.*}}, i32 1, <32 x i1> %{{.*}})
14031403
return _mm512_mask_storeu_epi16(__P, __U, __A);
14041404
}
14051405
__mmask64 test_mm512_test_epi8_mask(__m512i __A, __m512i __B) {
@@ -1410,7 +1410,7 @@ __mmask64 test_mm512_test_epi8_mask(__m512i __A, __m512i __B) {
14101410

14111411
void test_mm512_mask_storeu_epi8(void *__P, __mmask64 __U, __m512i __A) {
14121412
// CHECK-LABEL: @test_mm512_mask_storeu_epi8
1413-
// CHECK: @llvm.masked.store.v64i8(<64 x i8> %{{.*}}, <64 x i8>* %{{.*}}, i32 1, <64 x i1> %{{.*}})
1413+
// CHECK: @llvm.masked.store.v64i8.p0v64i8(<64 x i8> %{{.*}}, <64 x i8>* %{{.*}}, i32 1, <64 x i1> %{{.*}})
14141414
return _mm512_mask_storeu_epi8(__P, __U, __A);
14151415
}
14161416
__mmask64 test_mm512_mask_test_epi8_mask(__mmask64 __U, __m512i __A, __m512i __B) {

‎clang/test/CodeGen/avx512f-builtins.c‎

Lines changed: 18 additions & 18 deletions
Original file line numberDiff line numberDiff line change
@@ -186,7 +186,7 @@ void test_mm512_storeu_pd(void *p, __m512d a)
186186
void test_mm512_mask_store_ps(void *p, __m512 a, __mmask16 m)
187187
{
188188
// CHECK-LABEL: @test_mm512_mask_store_ps
189-
// CHECK: @llvm.masked.store.v16f32(<16 x float> %{{.*}}, <16 x float>* %{{.*}}, i32 64, <16 x i1> %{{.*}})
189+
// CHECK: @llvm.masked.store.v16f32.p0v16f32(<16 x float> %{{.*}}, <16 x float>* %{{.*}}, i32 64, <16 x i1> %{{.*}})
190190
_mm512_mask_store_ps(p, m, a);
191191
}
192192

@@ -237,19 +237,19 @@ void test_mm512_store_pd(void *p, __m512d a)
237237
void test_mm512_mask_store_pd(void *p, __m512d a, __mmask8 m)
238238
{
239239
// CHECK-LABEL: @test_mm512_mask_store_pd
240-
// CHECK: @llvm.masked.store.v8f64(<8 x double> %{{.*}}, <8 x double>* %{{.*}}, i32 64, <8 x i1> %{{.*}})
240+
// CHECK: @llvm.masked.store.v8f64.p0v8f64(<8 x double> %{{.*}}, <8 x double>* %{{.*}}, i32 64, <8 x i1> %{{.*}})
241241
_mm512_mask_store_pd(p, m, a);
242242
}
243243

244244
void test_mm512_mask_storeu_epi32(void *__P, __mmask16 __U, __m512i __A) {
245245
// CHECK-LABEL: @test_mm512_mask_storeu_epi32
246-
// CHECK: @llvm.masked.store.v16i32(<16 x i32> %{{.*}}, <16 x i32>* %{{.*}}, i32 1, <16 x i1> %{{.*}})
246+
// CHECK: @llvm.masked.store.v16i32.p0v16i32(<16 x i32> %{{.*}}, <16 x i32>* %{{.*}}, i32 1, <16 x i1> %{{.*}})
247247
return _mm512_mask_storeu_epi32(__P, __U, __A);
248248
}
249249

250250
void test_mm512_mask_storeu_epi64(void *__P, __mmask8 __U, __m512i __A) {
251251
// CHECK-LABEL: @test_mm512_mask_storeu_epi64
252-
// CHECK: @llvm.masked.store.v8i64(<8 x i64> %{{.*}}, <8 x i64>* %{{.*}}, i32 1, <8 x i1> %{{.*}})
252+
// CHECK: @llvm.masked.store.v8i64.p0v8i64(<8 x i64> %{{.*}}, <8 x i64>* %{{.*}}, i32 1, <8 x i1> %{{.*}})
253253
return _mm512_mask_storeu_epi64(__P, __U, __A);
254254
}
255255

@@ -263,14 +263,14 @@ __m512i test_mm512_loadu_si512 (void *__P)
263263
__m512i test_mm512_mask_loadu_epi32 (__m512i __W, __mmask16 __U, void *__P)
264264
{
265265
// CHECK-LABEL: @test_mm512_mask_loadu_epi32
266-
// CHECK: @llvm.masked.load.v16i32(<16 x i32>* %{{.*}}, i32 1, <16 x i1> %{{.*}}, <16 x i32> %{{.*}})
266+
// CHECK: @llvm.masked.load.v16i32.p0v16i32(<16 x i32>* %{{.*}}, i32 1, <16 x i1> %{{.*}}, <16 x i32> %{{.*}})
267267
return _mm512_mask_loadu_epi32 (__W,__U, __P);
268268
}
269269

270270
__m512i test_mm512_mask_loadu_epi64 (__m512i __W, __mmask8 __U, void *__P)
271271
{
272272
// CHECK-LABEL: @test_mm512_mask_loadu_epi64
273-
// CHECK: @llvm.masked.load.v8i64(<8 x i64>* %{{.*}}, i32 1, <8 x i1> %{{.*}}, <8 x i64> %{{.*}})
273+
// CHECK: @llvm.masked.load.v8i64.p0v8i64(<8 x i64>* %{{.*}}, i32 1, <8 x i1> %{{.*}}, <8 x i64> %{{.*}})
274274
return _mm512_mask_loadu_epi64 (__W,__U, __P);
275275
}
276276

@@ -284,7 +284,7 @@ __m512 test_mm512_loadu_ps(void *p)
284284
__m512 test_mm512_mask_loadu_ps (__m512 __W, __mmask16 __U, void *__P)
285285
{
286286
// CHECK-LABEL: @test_mm512_mask_loadu_ps
287-
// CHECK: @llvm.masked.load.v16f32(<16 x float>* %{{.*}}, i32 1, <16 x i1> %{{.*}}, <16 x float> %{{.*}})
287+
// CHECK: @llvm.masked.load.v16f32.p0v16f32(<16 x float>* %{{.*}}, i32 1, <16 x i1> %{{.*}}, <16 x float> %{{.*}})
288288
return _mm512_mask_loadu_ps (__W,__U, __P);
289289
}
290290

@@ -298,7 +298,7 @@ __m512d test_mm512_loadu_pd(void *p)
298298
__m512d test_mm512_mask_loadu_pd (__m512d __W, __mmask8 __U, void *__P)
299299
{
300300
// CHECK-LABEL: @test_mm512_mask_loadu_pd
301-
// CHECK: @llvm.masked.load.v8f64(<8 x double>* %{{.*}}, i32 1, <8 x i1> %{{.*}}, <8 x double> %{{.*}})
301+
// CHECK: @llvm.masked.load.v8f64.p0v8f64(<8 x double>* %{{.*}}, i32 1, <8 x i1> %{{.*}}, <8 x double> %{{.*}})
302302
return _mm512_mask_loadu_pd (__W,__U, __P);
303303
}
304304

@@ -339,14 +339,14 @@ __m512 test_mm512_load_ps(void *p)
339339
__m512 test_mm512_mask_load_ps (__m512 __W, __mmask16 __U, void *__P)
340340
{
341341
// CHECK-LABEL: @test_mm512_mask_load_ps
342-
// CHECK: @llvm.masked.load.v16f32(<16 x float>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x float> %{{.*}})
342+
// CHECK: @llvm.masked.load.v16f32.p0v16f32(<16 x float>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x float> %{{.*}})
343343
return _mm512_mask_load_ps (__W,__U, __P);
344344
}
345345

346346
__m512 test_mm512_maskz_load_ps(__mmask16 __U, void *__P)
347347
{
348348
// CHECK-LABEL: @test_mm512_maskz_load_ps
349-
// CHECK: @llvm.masked.load.v16f32(<16 x float>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x float> %{{.*}})
349+
// CHECK: @llvm.masked.load.v16f32.p0v16f32(<16 x float>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x float> %{{.*}})
350350
return _mm512_maskz_load_ps(__U, __P);
351351
}
352352

@@ -360,14 +360,14 @@ __m512d test_mm512_load_pd(void *p)
360360
__m512d test_mm512_mask_load_pd (__m512d __W, __mmask8 __U, void *__P)
361361
{
362362
// CHECK-LABEL: @test_mm512_mask_load_pd
363-
// CHECK: @llvm.masked.load.v8f64(<8 x double>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x double> %{{.*}})
363+
// CHECK: @llvm.masked.load.v8f64.p0v8f64(<8 x double>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x double> %{{.*}})
364364
return _mm512_mask_load_pd (__W,__U, __P);
365365
}
366366

367367
__m512d test_mm512_maskz_load_pd(__mmask8 __U, void *__P)
368368
{
369369
// CHECK-LABEL: @test_mm512_maskz_load_pd
370-
// CHECK: @llvm.masked.load.v8f64(<8 x double>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x double> %{{.*}})
370+
// CHECK: @llvm.masked.load.v8f64.p0v8f64(<8 x double>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x double> %{{.*}})
371371
return _mm512_maskz_load_pd(__U, __P);
372372
}
373373

@@ -2620,13 +2620,13 @@ __m512i test_mm512_maskz_srli_epi64(__mmask8 __U, __m512i __A) {
26202620

26212621
__m512i test_mm512_mask_load_epi32(__m512i __W, __mmask16 __U, void const *__P) {
26222622
// CHECK-LABEL: @test_mm512_mask_load_epi32
2623-
// CHECK: @llvm.masked.load.v16i32(<16 x i32>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x i32> %{{.*}})
2623+
// CHECK: @llvm.masked.load.v16i32.p0v16i32(<16 x i32>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x i32> %{{.*}})
26242624
return _mm512_mask_load_epi32(__W, __U, __P);
26252625
}
26262626

26272627
__m512i test_mm512_maskz_load_epi32(__mmask16 __U, void const *__P) {
26282628
// CHECK-LABEL: @test_mm512_maskz_load_epi32
2629-
// CHECK: @llvm.masked.load.v16i32(<16 x i32>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x i32> %{{.*}})
2629+
// CHECK: @llvm.masked.load.v16i32.p0v16i32(<16 x i32>* %{{.*}}, i32 64, <16 x i1> %{{.*}}, <16 x i32> %{{.*}})
26302630
return _mm512_maskz_load_epi32(__U, __P);
26312631
}
26322632

@@ -2656,25 +2656,25 @@ __m512i test_mm512_maskz_mov_epi64(__mmask8 __U, __m512i __A) {
26562656

26572657
__m512i test_mm512_mask_load_epi64(__m512i __W, __mmask8 __U, void const *__P) {
26582658
// CHECK-LABEL: @test_mm512_mask_load_epi64
2659-
// CHECK: @llvm.masked.load.v8i64(<8 x i64>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x i64> %{{.*}})
2659+
// CHECK: @llvm.masked.load.v8i64.p0v8i64(<8 x i64>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x i64> %{{.*}})
26602660
return _mm512_mask_load_epi64(__W, __U, __P);
26612661
}
26622662

26632663
__m512i test_mm512_maskz_load_epi64(__mmask8 __U, void const *__P) {
26642664
// CHECK-LABEL: @test_mm512_maskz_load_epi64
2665-
// CHECK: @llvm.masked.load.v8i64(<8 x i64>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x i64> %{{.*}})
2665+
// CHECK: @llvm.masked.load.v8i64.p0v8i64(<8 x i64>* %{{.*}}, i32 64, <8 x i1> %{{.*}}, <8 x i64> %{{.*}})
26662666
return _mm512_maskz_load_epi64(__U, __P);
26672667
}
26682668

26692669
void test_mm512_mask_store_epi32(void *__P, __mmask16 __U, __m512i __A) {
26702670
// CHECK-LABEL: @test_mm512_mask_store_epi32
2671-
// CHECK: @llvm.masked.store.v16i32(<16 x i32> %{{.*}}, <16 x i32>* %{{.*}}, i32 64, <16 x i1> %{{.*}})
2671+
// CHECK: @llvm.masked.store.v16i32.p0v16i32(<16 x i32> %{{.*}}, <16 x i32>* %{{.*}}, i32 64, <16 x i1> %{{.*}})
26722672
return _mm512_mask_store_epi32(__P, __U, __A);
26732673
}
26742674

26752675
void test_mm512_mask_store_epi64(void *__P, __mmask8 __U, __m512i __A) {
26762676
// CHECK-LABEL: @test_mm512_mask_store_epi64
2677-
// CHECK: @llvm.masked.store.v8i64(<8 x i64> %{{.*}}, <8 x i64>* %{{.*}}, i32 64, <8 x i1> %{{.*}})
2677+
// CHECK: @llvm.masked.store.v8i64.p0v8i64(<8 x i64> %{{.*}}, <8 x i64>* %{{.*}}, i32 64, <8 x i1> %{{.*}})
26782678
return _mm512_mask_store_epi64(__P, __U, __A);
26792679
}
26802680

0 commit comments

Comments
 (0)