Skip to content

Commit 9bcd58f

Browse files
andykaylorandykaylor
authored
[CIR] Fix compressstore builtin tests (#201902)
The llvm.masked.compressstore intrinsic was update to allow overloaded pointer arguments for address space support. This led to failures in the CIR tests that check for this intrinsic being called. This change updates the checks.
1 parent 3b98320 commit 9bcd58f

1 file changed

Lines changed: 17 additions & 17 deletions

File tree

‎clang/test/CIR/CodeGenBuiltins/X86/avx512vl-builtins.c‎

Lines changed: 17 additions & 17 deletions
Original file line numberDiff line numberDiff line change
@@ -732,78 +732,78 @@ void test_mm_mask_compressstoreu_pd(void *__P, __mmask8 __U, __m128d __A) {
732732
// CIR-LABEL: _mm_mask_compressstoreu_pd
733733
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<2 x !cir.double>, !cir.ptr<!cir.vector<2 x !cir.double>>, !cir.vector<2 x !cir.int<s, 1>>){{.*}}
734734
// LLVM-LABEL: @test_mm_mask_compressstoreu_pd
735-
// LLVM: @llvm.masked.compressstore.v2f64(<2 x double> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
735+
// LLVM: @llvm.masked.compressstore.v2f64.p0(<2 x double> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
736736
// OGCG-LABEL: @test_mm_mask_compressstoreu_pd
737-
// OGCG: @llvm.masked.compressstore.v2f64(<2 x double> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
737+
// OGCG: @llvm.masked.compressstore.v2f64.p0(<2 x double> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
738738
return _mm_mask_compressstoreu_pd(__P, __U, __A);
739739
}
740740

741741
void test_mm256_mask_compressstoreu_pd(void *__P, __mmask8 __U, __m256d __A) {
742742
// CIR-LABEL: _mm256_mask_compressstoreu_pd
743743
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<4 x !cir.double>, !cir.ptr<!cir.vector<4 x !cir.double>>, !cir.vector<4 x !cir.int<s, 1>>){{.*}}
744744
// LLVM-LABEL: @test_mm256_mask_compressstoreu_pd
745-
// LLVM: @llvm.masked.compressstore.v4f64(<4 x double> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
745+
// LLVM: @llvm.masked.compressstore.v4f64.p0(<4 x double> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
746746
// OGCG-LABEL: @test_mm256_mask_compressstoreu_pd
747-
// OGCG: @llvm.masked.compressstore.v4f64(<4 x double> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
747+
// OGCG: @llvm.masked.compressstore.v4f64.p0(<4 x double> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
748748
return _mm256_mask_compressstoreu_pd(__P, __U, __A);
749749
}
750750

751751
void test_mm_mask_compressstoreu_epi64(void *__P, __mmask8 __U, __m128i __A) {
752752
// CIR-LABEL: _mm_mask_compressstoreu_epi64
753753
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<2 x !s64i>, !cir.ptr<!cir.vector<2 x !s64i>>, !cir.vector<2 x !cir.int<s, 1>>){{.*}}
754754
// LLVM-LABEL: @test_mm_mask_compressstoreu_epi64
755-
// LLVM: @llvm.masked.compressstore.v2i64(<2 x i64> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
755+
// LLVM: @llvm.masked.compressstore.v2i64.p0(<2 x i64> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
756756
// OGCG-LABEL: @test_mm_mask_compressstoreu_epi64
757-
// OGCG: @llvm.masked.compressstore.v2i64(<2 x i64> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
757+
// OGCG: @llvm.masked.compressstore.v2i64.p0(<2 x i64> %{{.*}}, ptr %{{.*}}, <2 x i1> %{{.*}})
758758
return _mm_mask_compressstoreu_epi64(__P, __U, __A);
759759
}
760760

761761
void test_mm256_mask_compressstoreu_epi64(void *__P, __mmask8 __U, __m256i __A) {
762762
// CIR-LABEL: _mm256_mask_compressstoreu_epi64
763763
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<4 x !s64i>, !cir.ptr<!cir.vector<4 x !s64i>>, !cir.vector<4 x !cir.int<s, 1>>){{.*}}
764764
// LLVM-LABEL: @test_mm256_mask_compressstoreu_epi64
765-
// LLVM: @llvm.masked.compressstore.v4i64(<4 x i64> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
765+
// LLVM: @llvm.masked.compressstore.v4i64.p0(<4 x i64> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
766766
// OGCG-LABEL: @test_mm256_mask_compressstoreu_epi64
767-
// OGCG: @llvm.masked.compressstore.v4i64(<4 x i64> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
767+
// OGCG: @llvm.masked.compressstore.v4i64.p0(<4 x i64> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
768768
return _mm256_mask_compressstoreu_epi64(__P, __U, __A);
769769
}
770770

771771
void test_mm_mask_compressstoreu_ps(void *__P, __mmask8 __U, __m128 __A) {
772772
// CIR-LABEL: _mm_mask_compressstoreu_ps
773773
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<4 x !cir.float>, !cir.ptr<!cir.vector<4 x !cir.float>>, !cir.vector<4 x !cir.int<s, 1>>){{.*}}
774774
// LLVM-LABEL: @test_mm_mask_compressstoreu_ps
775-
// LLVM: @llvm.masked.compressstore.v4f32(<4 x float> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
775+
// LLVM: @llvm.masked.compressstore.v4f32.p0(<4 x float> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
776776
// OGCG-LABEL: @test_mm_mask_compressstoreu_ps
777-
// OGCG: @llvm.masked.compressstore.v4f32(<4 x float> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
777+
// OGCG: @llvm.masked.compressstore.v4f32.p0(<4 x float> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
778778
return _mm_mask_compressstoreu_ps(__P, __U, __A);
779779
}
780780

781781
void test_mm256_mask_compressstoreu_ps(void *__P, __mmask8 __U, __m256 __A) {
782782
// CIR-LABEL: _mm256_mask_compressstoreu_ps
783783
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<8 x !cir.float>, !cir.ptr<!cir.vector<8 x !cir.float>>, !cir.vector<8 x !cir.int<s, 1>>){{.*}}
784784
// LLVM-LABEL: @test_mm256_mask_compressstoreu_ps
785-
// LLVM: @llvm.masked.compressstore.v8f32(<8 x float> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
785+
// LLVM: @llvm.masked.compressstore.v8f32.p0(<8 x float> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
786786
// OGCG-LABEL: @test_mm256_mask_compressstoreu_ps
787-
// OGCG: @llvm.masked.compressstore.v8f32(<8 x float> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
787+
// OGCG: @llvm.masked.compressstore.v8f32.p0(<8 x float> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
788788
return _mm256_mask_compressstoreu_ps(__P, __U, __A);
789789
}
790790

791791
void test_mm_mask_compressstoreu_epi32(void *__P, __mmask8 __U, __m128i __A) {
792792
// CIR-LABEL: _mm_mask_compressstoreu_epi32
793793
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<4 x !s32i>, !cir.ptr<!cir.vector<4 x !s32i>>, !cir.vector<4 x !cir.int<s, 1>>){{.*}}
794794
// LLVM-LABEL: @test_mm_mask_compressstoreu_epi32
795-
// LLVM: @llvm.masked.compressstore.v4i32(<4 x i32> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
795+
// LLVM: @llvm.masked.compressstore.v4i32.p0(<4 x i32> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
796796
// OGCG-LABEL: @test_mm_mask_compressstoreu_epi32
797-
// OGCG: @llvm.masked.compressstore.v4i32(<4 x i32> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
797+
// OGCG: @llvm.masked.compressstore.v4i32.p0(<4 x i32> %{{.*}}, ptr %{{.*}}, <4 x i1> %{{.*}})
798798
return _mm_mask_compressstoreu_epi32(__P, __U, __A);
799799
}
800800

801801
void test_mm256_mask_compressstoreu_epi32(void *__P, __mmask8 __U, __m256i __A) {
802802
// CIR-LABEL: _mm256_mask_compressstoreu_epi32
803803
// CIR: cir.call_llvm_intrinsic "masked.compressstore" %{{.*}}, %{{.*}}, %{{.*}} : (!cir.vector<8 x !s32i>, !cir.ptr<!cir.vector<8 x !s32i>>, !cir.vector<8 x !cir.int<s, 1>>){{.*}}
804804
// LLVM-LABEL: @test_mm256_mask_compressstoreu_epi32
805-
// LLVM: @llvm.masked.compressstore.v8i32(<8 x i32> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
805+
// LLVM: @llvm.masked.compressstore.v8i32.p0(<8 x i32> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
806806
// OGCG-LABEL: @test_mm256_mask_compressstoreu_epi32
807-
// OGCG: @llvm.masked.compressstore.v8i32(<8 x i32> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
807+
// OGCG: @llvm.masked.compressstore.v8i32.p0(<8 x i32> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
808808
return _mm256_mask_compressstoreu_epi32(__P, __U, __A);
809-
}
809+
}

0 commit comments

Comments
 (0)