Skip to content

Commit d9452c3

Browse files
eugeneepshteyneugeneepshteyn
authored
Merge branch 'llvm:main' into copy-inout-dev
2 parents 889f7c1 + 44aedac commit d9452c3

File tree

112 files changed

+2501
-1285
lines changed

Some content is hidden

Large Commits have some content hidden by default. Use the searchbox below for content that may be hidden.

112 files changed

+2501
-1285
lines changed

‎.ci/monolithic-linux.sh

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -29,7 +29,7 @@ runtime_targets="${4}"
2929
runtime_targets_needs_reconfig="${5}"
3030
enable_cir="${6}"
3131

32-
lit_args="-v --xunit-xml-output ${BUILD_DIR}/test-results.xml --use-unique-output-file-name --timeout=1200 --time-tests"
32+
lit_args="-v --xunit-xml-output ${BUILD_DIR}/test-results.xml --use-unique-output-file-name --timeout=1200 --time-tests --succinct"
3333

3434
start-group "CMake"
3535
export PIP_BREAK_SYSTEM_PACKAGES=1

‎.ci/monolithic-windows.sh

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -39,7 +39,7 @@ cmake -S "${MONOREPO_ROOT}"/llvm -B "${BUILD_DIR}" \
3939
-D LLVM_ENABLE_ASSERTIONS=ON \
4040
-D LLVM_BUILD_EXAMPLES=ON \
4141
-D COMPILER_RT_BUILD_LIBFUZZER=OFF \
42-
-D LLVM_LIT_ARGS="-v --xunit-xml-output ${BUILD_DIR}/test-results.xml --use-unique-output-file-name --timeout=1200 --time-tests" \
42+
-D LLVM_LIT_ARGS="-v --xunit-xml-output ${BUILD_DIR}/test-results.xml --use-unique-output-file-name --timeout=1200 --time-tests --succinct" \
4343
-D COMPILER_RT_BUILD_ORC=OFF \
4444
-D CMAKE_C_COMPILER_LAUNCHER=sccache \
4545
-D CMAKE_CXX_COMPILER_LAUNCHER=sccache \

‎.github/workflows/mlir-spirv-tests.yml

Lines changed: 32 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,32 @@
1+
name: MLIR SPIR-V Tests
2+
3+
permissions:
4+
contents: read
5+
6+
on:
7+
workflow_dispatch:
8+
pull_request:
9+
paths:
10+
- 'mlir/include/mlir/Dialect/SPIRV/**'
11+
- 'mlir/lib/Dialect/SPIRV/**'
12+
- 'mlir/include/mlir/Target/SPIRV/**'
13+
- 'mlir/lib/Target/SPIRV/**'
14+
- 'mlir/test/Target/SPIRV/**'
15+
- '.github/workflows/mlir-spirv-tests.yml'
16+
17+
concurrency:
18+
# Skip intermediate builds: always.
19+
# Cancel intermediate builds: only if it is a pull request build.
20+
group: ${{ github.workflow }}-${{ github.ref }}
21+
cancel-in-progress: ${{ startsWith(github.ref, 'refs/pull/') }}
22+
23+
jobs:
24+
check_spirv:
25+
if: github.repository_owner == 'llvm'
26+
name: Test MLIR SPIR-V
27+
uses: ./.github/workflows/llvm-project-tests.yml
28+
with:
29+
build_target: check-mlir
30+
projects: mlir
31+
extra_cmake_args: '-DLLVM_TARGETS_TO_BUILD="host" -DLLVM_INCLUDE_SPIRV_TOOLS_TESTS=ON'
32+
os_list: '["ubuntu-24.04"]'

‎clang/lib/AST/ByteCode/DynamicAllocator.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -128,7 +128,7 @@ bool DynamicAllocator::deallocate(const Expr *Source,
128128
return false;
129129

130130
auto &Site = It->second;
131-
assert(Site.size() > 0);
131+
assert(!Site.empty());
132132

133133
// Find the Block to delete.
134134
auto AllocIt = llvm::find_if(Site.Allocations, [&](const Allocation &A) {
@@ -144,7 +144,7 @@ bool DynamicAllocator::deallocate(const Expr *Source,
144144
S.deallocate(B);
145145
Site.Allocations.erase(AllocIt);
146146

147-
if (Site.size() == 0)
147+
if (Site.empty())
148148
AllocationSites.erase(It);
149149

150150
return true;

‎clang/lib/AST/ByteCode/DynamicAllocator.h

Lines changed: 3 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -55,6 +55,7 @@ class DynamicAllocator final {
5555
}
5656

5757
size_t size() const { return Allocations.size(); }
58+
bool empty() const { return Allocations.empty(); }
5859
};
5960

6061
public:
@@ -65,8 +66,6 @@ class DynamicAllocator final {
6566

6667
void cleanup();
6768

68-
unsigned getNumAllocations() const { return AllocationSites.size(); }
69-
7069
/// Allocate ONE element of the given descriptor.
7170
Block *allocate(const Descriptor *D, unsigned EvalID, Form AllocForm);
7271
/// Allocate \p NumElements primitive elements of the given type.
@@ -96,6 +95,8 @@ class DynamicAllocator final {
9695
return llvm::make_range(AllocationSites.begin(), AllocationSites.end());
9796
}
9897

98+
bool hasAllocations() const { return !AllocationSites.empty(); }
99+
99100
private:
100101
llvm::DenseMap<const Expr *, AllocationSite> AllocationSites;
101102

‎clang/lib/AST/ByteCode/InterpState.cpp

Lines changed: 4 additions & 5 deletions
Original file line numberDiff line numberDiff line change
@@ -101,15 +101,14 @@ void InterpState::deallocate(Block *B) {
101101
}
102102

103103
bool InterpState::maybeDiagnoseDanglingAllocations() {
104-
bool NoAllocationsLeft = (Alloc.getNumAllocations() == 0);
104+
bool NoAllocationsLeft = !Alloc.hasAllocations();
105105

106106
if (!checkingPotentialConstantExpression()) {
107-
for (const auto &It : Alloc.allocation_sites()) {
108-
assert(It.second.size() > 0);
107+
for (const auto &[Source, Site] : Alloc.allocation_sites()) {
108+
assert(!Site.empty());
109109

110-
const Expr *Source = It.first;
111110
CCEDiag(Source->getExprLoc(), diag::note_constexpr_memory_leak)
112-
<< (It.second.size() - 1) << Source->getSourceRange();
111+
<< (Site.size() - 1) << Source->getSourceRange();
113112
}
114113
}
115114
// Keep evaluating before C++20, since the CXXNewExpr wasn't valid there

‎clang/lib/Sema/SemaTemplate.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -367,7 +367,7 @@ bool Sema::DiagnoseUnknownTemplateName(const IdentifierInfo &II,
367367

368368
// The code is missing a 'template' keyword prior to the dependent template
369369
// name.
370-
NestedNameSpecifier *Qualifier = (NestedNameSpecifier *)SS->getScopeRep();
370+
NestedNameSpecifier *Qualifier = SS->getScopeRep();
371371
SuggestedTemplate = TemplateTy::make(Context.getDependentTemplateName(
372372
{Qualifier, &II, /*HasTemplateKeyword=*/false}));
373373
Diag(IILoc, diag::err_template_kw_missing)

‎clang/test/CodeGen/X86/avx512-reduceIntrin.c

Lines changed: 51 additions & 48 deletions
Original file line numberDiff line numberDiff line change
@@ -1,171 +1,174 @@
1-
// RUN: %clang_cc1 -ffreestanding %s -O0 -triple=x86_64-apple-darwin -target-cpu skylake-avx512 -emit-llvm -o - -Wall -Werror | FileCheck %s
1+
// RUN: %clang_cc1 -x c -ffreestanding %s -O0 -triple=x86_64-apple-darwin -target-cpu skylake-avx512 -emit-llvm -o - -Wall -Werror | FileCheck %s
2+
// RUN: %clang_cc1 -x c -ffreestanding %s -O0 -triple=i386-apple-darwin -target-cpu skylake-avx512 -emit-llvm -o - -Wall -Werror | FileCheck %s
3+
// RUN: %clang_cc1 -x c++ -ffreestanding %s -O0 -triple=x86_64-apple-darwin -target-cpu skylake-avx512 -emit-llvm -o - -Wall -Werror | FileCheck %s
4+
// RUN: %clang_cc1 -x c++ -ffreestanding %s -O0 -triple=i386-apple-darwin -target-cpu skylake-avx512 -emit-llvm -o - -Wall -Werror | FileCheck %s
25

36
#include <immintrin.h>
47
#include "builtin_test_helpers.h"
58

69
long long test_mm512_reduce_add_epi64(__m512i __W){
7-
// CHECK-LABEL: @test_mm512_reduce_add_epi64(
8-
// CHECK: call i64 @llvm.vector.reduce.add.v8i64(<8 x i64> %{{.*}})
10+
// CHECK-LABEL: test_mm512_reduce_add_epi64
11+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.add.v8i64(<8 x i64> %{{.*}})
912
return _mm512_reduce_add_epi64(__W);
1013
}
1114
TEST_CONSTEXPR(_mm512_reduce_add_epi64((__m512i)(__v8di){-4, -3, -2, -1, 0, 1, 2, 3}) == -4);
1215

1316
long long test_mm512_reduce_mul_epi64(__m512i __W){
14-
// CHECK-LABEL: @test_mm512_reduce_mul_epi64(
15-
// CHECK: call i64 @llvm.vector.reduce.mul.v8i64(<8 x i64> %{{.*}})
17+
// CHECK-LABEL: test_mm512_reduce_mul_epi64
18+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.mul.v8i64(<8 x i64> %{{.*}})
1619
return _mm512_reduce_mul_epi64(__W);
1720
}
1821
TEST_CONSTEXPR(_mm512_reduce_mul_epi64((__m512i)(__v8di){1, 2, 3, 4, 5, 6, 7, 8}) == 40320);
1922

2023
long long test_mm512_reduce_or_epi64(__m512i __W){
21-
// CHECK-LABEL: @test_mm512_reduce_or_epi64(
22-
// CHECK: call i64 @llvm.vector.reduce.or.v8i64(<8 x i64> %{{.*}})
24+
// CHECK-LABEL: test_mm512_reduce_or_epi64
25+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.or.v8i64(<8 x i64> %{{.*}})
2326
return _mm512_reduce_or_epi64(__W);
2427
}
2528
TEST_CONSTEXPR(_mm512_reduce_or_epi64((__m512i)(__v8di){0x100, 0x200, 0x400, 0x800, 0, 0, 0, 0}) == 0xF00);
2629

2730
long long test_mm512_reduce_and_epi64(__m512i __W){
28-
// CHECK-LABEL: @test_mm512_reduce_and_epi64(
29-
// CHECK: call i64 @llvm.vector.reduce.and.v8i64(<8 x i64> %{{.*}})
31+
// CHECK-LABEL: test_mm512_reduce_and_epi64
32+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.and.v8i64(<8 x i64> %{{.*}})
3033
return _mm512_reduce_and_epi64(__W);
3134
}
3235
TEST_CONSTEXPR(_mm512_reduce_and_epi64((__m512i)(__v8di){0xFFFF, 0xFF00, 0x00FF, 0xFFFF, 0xFFFF, 0xFFFF, 0xFF00, 0x00FF}) == 0x0000);
3336

3437
long long test_mm512_mask_reduce_add_epi64(__mmask8 __M, __m512i __W){
35-
// CHECK-LABEL: @test_mm512_mask_reduce_add_epi64(
38+
// CHECK-LABEL: test_mm512_mask_reduce_add_epi64
3639
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
37-
// CHECK: call i64 @llvm.vector.reduce.add.v8i64(<8 x i64> %{{.*}})
40+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.add.v8i64(<8 x i64> %{{.*}})
3841
return _mm512_mask_reduce_add_epi64(__M, __W);
3942
}
4043

4144
long long test_mm512_mask_reduce_mul_epi64(__mmask8 __M, __m512i __W){
42-
// CHECK-LABEL: @test_mm512_mask_reduce_mul_epi64(
45+
// CHECK-LABEL: test_mm512_mask_reduce_mul_epi64
4346
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
44-
// CHECK: call i64 @llvm.vector.reduce.mul.v8i64(<8 x i64> %{{.*}})
47+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.mul.v8i64(<8 x i64> %{{.*}})
4548
return _mm512_mask_reduce_mul_epi64(__M, __W);
4649
}
4750

4851
long long test_mm512_mask_reduce_and_epi64(__mmask8 __M, __m512i __W){
49-
// CHECK-LABEL: @test_mm512_mask_reduce_and_epi64(
52+
// CHECK-LABEL: test_mm512_mask_reduce_and_epi64
5053
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
51-
// CHECK: call i64 @llvm.vector.reduce.and.v8i64(<8 x i64> %{{.*}})
54+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.and.v8i64(<8 x i64> %{{.*}})
5255
return _mm512_mask_reduce_and_epi64(__M, __W);
5356
}
5457

5558
long long test_mm512_mask_reduce_or_epi64(__mmask8 __M, __m512i __W){
56-
// CHECK-LABEL: @test_mm512_mask_reduce_or_epi64(
59+
// CHECK-LABEL: test_mm512_mask_reduce_or_epi64
5760
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
58-
// CHECK: call i64 @llvm.vector.reduce.or.v8i64(<8 x i64> %{{.*}})
61+
// CHECK: call {{.*}}i64 @llvm.vector.reduce.or.v8i64(<8 x i64> %{{.*}})
5962
return _mm512_mask_reduce_or_epi64(__M, __W);
6063
}
6164

6265
int test_mm512_reduce_add_epi32(__m512i __W){
63-
// CHECK-LABEL: @test_mm512_reduce_add_epi32(
64-
// CHECK: call i32 @llvm.vector.reduce.add.v16i32(<16 x i32> %{{.*}})
66+
// CHECK-LABEL: test_mm512_reduce_add_epi32
67+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.add.v16i32(<16 x i32> %{{.*}})
6568
return _mm512_reduce_add_epi32(__W);
6669
}
6770
TEST_CONSTEXPR(_mm512_reduce_add_epi32((__m512i)(__v16si){-8, -7, -6, -5, -4, -3, -2, -1, 0, 1, 2, 3, 4, 5, 6, 7}) == -8);
6871

6972
int test_mm512_reduce_mul_epi32(__m512i __W){
70-
// CHECK-LABEL: @test_mm512_reduce_mul_epi32(
71-
// CHECK: call i32 @llvm.vector.reduce.mul.v16i32(<16 x i32> %{{.*}})
73+
// CHECK-LABEL: test_mm512_reduce_mul_epi32
74+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.mul.v16i32(<16 x i32> %{{.*}})
7275
return _mm512_reduce_mul_epi32(__W);
7376
}
7477
TEST_CONSTEXPR(_mm512_reduce_mul_epi32((__m512i)(__v16si){1, 1, 1, 1, 1, 1, 1, 1, 2, 2, 3, 1, 1, -3, 1, 1}) == -36);
7578

7679
int test_mm512_reduce_or_epi32(__m512i __W){
77-
// CHECK: call i32 @llvm.vector.reduce.or.v16i32(<16 x i32> %{{.*}})
80+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.or.v16i32(<16 x i32> %{{.*}})
7881
return _mm512_reduce_or_epi32(__W);
7982
}
8083
TEST_CONSTEXPR(_mm512_reduce_or_epi32((__m512i)(__v16si){0x01, 0x02, 0x04, 0x08, 0x10, 0x20, 0x40, 0x80, 0, 0, 0, 0, 0, 0, 0, 0}) == 0xFF);
8184

8285
int test_mm512_reduce_and_epi32(__m512i __W){
83-
// CHECK-LABEL: @test_mm512_reduce_and_epi32(
84-
// CHECK: call i32 @llvm.vector.reduce.and.v16i32(<16 x i32> %{{.*}})
86+
// CHECK-LABEL: test_mm512_reduce_and_epi32
87+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.and.v16i32(<16 x i32> %{{.*}})
8588
return _mm512_reduce_and_epi32(__W);
8689
}
8790
TEST_CONSTEXPR(_mm512_reduce_and_epi32((__m512i)(__v16si){0xFF, 0xF0, 0x0F, 0xFF, 0xFF, 0xFF, 0xF0, 0x0F, 0xFF, 0xFF, 0xFF, 0xFF, 0xF0, 0xF0, 0x0F, 0x0F}) == 0x00);
8891

8992
int test_mm512_mask_reduce_add_epi32(__mmask16 __M, __m512i __W){
90-
// CHECK-LABEL: @test_mm512_mask_reduce_add_epi32(
93+
// CHECK-LABEL: test_mm512_mask_reduce_add_epi32
9194
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
92-
// CHECK: call i32 @llvm.vector.reduce.add.v16i32(<16 x i32> %{{.*}})
95+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.add.v16i32(<16 x i32> %{{.*}})
9396
return _mm512_mask_reduce_add_epi32(__M, __W);
9497
}
9598

9699
int test_mm512_mask_reduce_mul_epi32(__mmask16 __M, __m512i __W){
97-
// CHECK-LABEL: @test_mm512_mask_reduce_mul_epi32(
100+
// CHECK-LABEL: test_mm512_mask_reduce_mul_epi32
98101
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
99-
// CHECK: call i32 @llvm.vector.reduce.mul.v16i32(<16 x i32> %{{.*}})
102+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.mul.v16i32(<16 x i32> %{{.*}})
100103
return _mm512_mask_reduce_mul_epi32(__M, __W);
101104
}
102105

103106
int test_mm512_mask_reduce_and_epi32(__mmask16 __M, __m512i __W){
104-
// CHECK-LABEL: @test_mm512_mask_reduce_and_epi32(
107+
// CHECK-LABEL: test_mm512_mask_reduce_and_epi32
105108
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
106-
// CHECK: call i32 @llvm.vector.reduce.and.v16i32(<16 x i32> %{{.*}})
109+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.and.v16i32(<16 x i32> %{{.*}})
107110
return _mm512_mask_reduce_and_epi32(__M, __W);
108111
}
109112

110113
int test_mm512_mask_reduce_or_epi32(__mmask16 __M, __m512i __W){
111-
// CHECK-LABEL: @test_mm512_mask_reduce_or_epi32(
114+
// CHECK-LABEL: test_mm512_mask_reduce_or_epi32
112115
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
113-
// CHECK: call i32 @llvm.vector.reduce.or.v16i32(<16 x i32> %{{.*}})
116+
// CHECK: call {{.*}}i32 @llvm.vector.reduce.or.v16i32(<16 x i32> %{{.*}})
114117
return _mm512_mask_reduce_or_epi32(__M, __W);
115118
}
116119

117120
double test_mm512_reduce_add_pd(__m512d __W, double ExtraAddOp){
118-
// CHECK-LABEL: @test_mm512_reduce_add_pd(
121+
// CHECK-LABEL: test_mm512_reduce_add_pd
119122
// CHECK-NOT: reassoc
120-
// CHECK: call reassoc double @llvm.vector.reduce.fadd.v8f64(double -0.000000e+00, <8 x double> %{{.*}})
123+
// CHECK: call reassoc {{.*}}double @llvm.vector.reduce.fadd.v8f64(double -0.000000e+00, <8 x double> %{{.*}})
121124
// CHECK-NOT: reassoc
122125
return _mm512_reduce_add_pd(__W) + ExtraAddOp;
123126
}
124127

125128
double test_mm512_reduce_mul_pd(__m512d __W, double ExtraMulOp){
126-
// CHECK-LABEL: @test_mm512_reduce_mul_pd(
129+
// CHECK-LABEL: test_mm512_reduce_mul_pd
127130
// CHECK-NOT: reassoc
128-
// CHECK: call reassoc double @llvm.vector.reduce.fmul.v8f64(double 1.000000e+00, <8 x double> %{{.*}})
131+
// CHECK: call reassoc {{.*}}double @llvm.vector.reduce.fmul.v8f64(double 1.000000e+00, <8 x double> %{{.*}})
129132
// CHECK-NOT: reassoc
130133
return _mm512_reduce_mul_pd(__W) * ExtraMulOp;
131134
}
132135

133136
float test_mm512_reduce_add_ps(__m512 __W){
134-
// CHECK-LABEL: @test_mm512_reduce_add_ps(
135-
// CHECK: call reassoc float @llvm.vector.reduce.fadd.v16f32(float -0.000000e+00, <16 x float> %{{.*}})
137+
// CHECK-LABEL: test_mm512_reduce_add_ps
138+
// CHECK: call reassoc {{.*}}float @llvm.vector.reduce.fadd.v16f32(float -0.000000e+00, <16 x float> %{{.*}})
136139
return _mm512_reduce_add_ps(__W);
137140
}
138141

139142
float test_mm512_reduce_mul_ps(__m512 __W){
140-
// CHECK-LABEL: @test_mm512_reduce_mul_ps(
141-
// CHECK: call reassoc float @llvm.vector.reduce.fmul.v16f32(float 1.000000e+00, <16 x float> %{{.*}})
143+
// CHECK-LABEL: test_mm512_reduce_mul_ps
144+
// CHECK: call reassoc {{.*}}float @llvm.vector.reduce.fmul.v16f32(float 1.000000e+00, <16 x float> %{{.*}})
142145
return _mm512_reduce_mul_ps(__W);
143146
}
144147

145148
double test_mm512_mask_reduce_add_pd(__mmask8 __M, __m512d __W){
146-
// CHECK-LABEL: @test_mm512_mask_reduce_add_pd(
149+
// CHECK-LABEL: test_mm512_mask_reduce_add_pd
147150
// CHECK: select <8 x i1> %{{.*}}, <8 x double> %{{.*}}, <8 x double> %{{.*}}
148-
// CHECK: call reassoc double @llvm.vector.reduce.fadd.v8f64(double -0.000000e+00, <8 x double> %{{.*}})
151+
// CHECK: call reassoc {{.*}}double @llvm.vector.reduce.fadd.v8f64(double -0.000000e+00, <8 x double> %{{.*}})
149152
return _mm512_mask_reduce_add_pd(__M, __W);
150153
}
151154

152155
double test_mm512_mask_reduce_mul_pd(__mmask8 __M, __m512d __W){
153-
// CHECK-LABEL: @test_mm512_mask_reduce_mul_pd(
156+
// CHECK-LABEL: test_mm512_mask_reduce_mul_pd
154157
// CHECK: select <8 x i1> %{{.*}}, <8 x double> %{{.*}}, <8 x double> %{{.*}}
155-
// CHECK: call reassoc double @llvm.vector.reduce.fmul.v8f64(double 1.000000e+00, <8 x double> %{{.*}})
158+
// CHECK: call reassoc {{.*}}double @llvm.vector.reduce.fmul.v8f64(double 1.000000e+00, <8 x double> %{{.*}})
156159
return _mm512_mask_reduce_mul_pd(__M, __W);
157160
}
158161

159162
float test_mm512_mask_reduce_add_ps(__mmask16 __M, __m512 __W){
160-
// CHECK-LABEL: @test_mm512_mask_reduce_add_ps(
163+
// CHECK-LABEL: test_mm512_mask_reduce_add_ps
161164
// CHECK: select <16 x i1> %{{.*}}, <16 x float> {{.*}}, <16 x float> {{.*}}
162-
// CHECK: call reassoc float @llvm.vector.reduce.fadd.v16f32(float -0.000000e+00, <16 x float> %{{.*}})
165+
// CHECK: call reassoc {{.*}}float @llvm.vector.reduce.fadd.v16f32(float -0.000000e+00, <16 x float> %{{.*}})
163166
return _mm512_mask_reduce_add_ps(__M, __W);
164167
}
165168

166169
float test_mm512_mask_reduce_mul_ps(__mmask16 __M, __m512 __W){
167-
// CHECK-LABEL: @test_mm512_mask_reduce_mul_ps(
170+
// CHECK-LABEL: test_mm512_mask_reduce_mul_ps
168171
// CHECK: select <16 x i1> %{{.*}}, <16 x float> {{.*}}, <16 x float> %{{.*}}
169-
// CHECK: call reassoc float @llvm.vector.reduce.fmul.v16f32(float 1.000000e+00, <16 x float> %{{.*}})
172+
// CHECK: call reassoc {{.*}}float @llvm.vector.reduce.fmul.v16f32(float 1.000000e+00, <16 x float> %{{.*}})
170173
return _mm512_mask_reduce_mul_ps(__M, __W);
171174
}

0 commit comments

Comments
 (0)