| // RUN: %clang_cc1 %s -flax-vector-conversions=none -ffreestanding -triple=x86_64 -target-feature +avx10.2 \ |
| // RUN: -emit-llvm -o - -Wno-invalid-feature-combination -Wall -Werror | FileCheck %s |
| // RUN: %clang_cc1 %s -flax-vector-conversions=none -ffreestanding -triple=i386 -target-feature +avx10.2 \ |
| // RUN: -emit-llvm -o - -Wno-invalid-feature-combination -Wall -Werror | FileCheck %s |
| |
| #include <immintrin.h> |
| |
| __m128bh test_mm_minmax_pbh(__m128bh __A, __m128bh __B) { |
| // CHECK-LABEL: @test_mm_minmax_pbh( |
| // CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxbf16128( |
| return _mm_minmax_pbh(__A, __B, 127); |
| } |
| |
| __m128bh test_mm_mask_minmax_pbh(__m128bh __A, __mmask8 __B, __m128bh __C, __m128bh __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_pbh( |
| // CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxbf16128( |
| // CHECK: select <8 x i1> %{{.*}}, <8 x bfloat> %{{.*}}, <8 x bfloat> %{{.*}} |
| return _mm_mask_minmax_pbh(__A, __B, __C, __D, 127); |
| } |
| |
| __m128bh test_mm_maskz_minmax_pbh(__mmask8 __A, __m128bh __B, __m128bh __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_pbh( |
| // CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxbf16128( |
| // CHECK: zeroinitializer |
| // CHECK: select <8 x i1> %{{.*}}, <8 x bfloat> %{{.*}}, <8 x bfloat> %{{.*}} |
| return _mm_maskz_minmax_pbh(__A, __B, __C, 127); |
| } |
| |
| __m256bh test_mm256_minmax_pbh(__m256bh __A, __m256bh __B) { |
| // CHECK-LABEL: @test_mm256_minmax_pbh( |
| // CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxbf16256( |
| return _mm256_minmax_pbh(__A, __B, 127); |
| } |
| |
| __m256bh test_mm256_mask_minmax_pbh(__m256bh __A, __mmask16 __B, __m256bh __C, __m256bh __D) { |
| // CHECK-LABEL: @test_mm256_mask_minmax_pbh( |
| // CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxbf16256( |
| // CHECK: select <16 x i1> %{{.*}}, <16 x bfloat> %{{.*}}, <16 x bfloat> %{{.*}} |
| return _mm256_mask_minmax_pbh(__A, __B, __C, __D, 127); |
| } |
| |
| __m256bh test_mm256_maskz_minmax_pbh(__mmask16 __A, __m256bh __B, __m256bh __C) { |
| // CHECK-LABEL: @test_mm256_maskz_minmax_pbh( |
| // CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxbf16256( |
| // CHECK: zeroinitializer |
| // CHECK: select <16 x i1> %{{.*}}, <16 x bfloat> %{{.*}}, <16 x bfloat> %{{.*}} |
| return _mm256_maskz_minmax_pbh(__A, __B, __C, 127); |
| } |
| |
| __m128d test_mm_minmax_pd(__m128d __A, __m128d __B) { |
| // CHECK-LABEL: @test_mm_minmax_pd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxpd128( |
| return _mm_minmax_pd(__A, __B, 127); |
| } |
| |
| __m128d test_mm_mask_minmax_pd(__m128d __A, __mmask8 __B, __m128d __C, __m128d __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_pd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxpd128( |
| return _mm_mask_minmax_pd(__A, __B, __C, __D, 127); |
| } |
| |
| __m128d test_mm_maskz_minmax_pd(__mmask8 __A, __m128d __B, __m128d __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_pd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxpd128( |
| return _mm_maskz_minmax_pd(__A, __B, __C, 127); |
| } |
| |
| __m256d test_mm256_minmax_pd(__m256d __A, __m256d __B) { |
| // CHECK-LABEL: @test_mm256_minmax_pd( |
| // CHECK: call <4 x double> @llvm.x86.avx10.mask.vminmaxpd256( |
| return _mm256_minmax_pd(__A, __B, 127); |
| } |
| |
| __m256d test_mm256_mask_minmax_pd(__m256d __A, __mmask8 __B, __m256d __C, __m256d __D) { |
| // CHECK-LABEL: @test_mm256_mask_minmax_pd( |
| // CHECK: call <4 x double> @llvm.x86.avx10.mask.vminmaxpd256( |
| return _mm256_mask_minmax_pd(__A, __B, __C, __D, 127); |
| } |
| |
| __m256d test_mm256_maskz_minmax_pd(__mmask8 __A, __m256d __B, __m256d __C) { |
| // CHECK-LABEL: @test_mm256_maskz_minmax_pd( |
| // CHECK: call <4 x double> @llvm.x86.avx10.mask.vminmaxpd256( |
| return _mm256_maskz_minmax_pd(__A, __B, __C, 127); |
| } |
| |
| __m128h test_mm_minmax_ph(__m128h __A, __m128h __B) { |
| // CHECK-LABEL: @test_mm_minmax_ph( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxph128( |
| return _mm_minmax_ph(__A, __B, 127); |
| } |
| |
| __m128h test_mm_mask_minmax_ph(__m128h __A, __mmask8 __B, __m128h __C, __m128h __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_ph( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxph128( |
| return _mm_mask_minmax_ph(__A, __B, __C, __D, 127); |
| } |
| |
| __m128h test_mm_maskz_minmax_ph(__mmask8 __A, __m128h __B, __m128h __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_ph( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxph128( |
| return _mm_maskz_minmax_ph(__A, __B, __C, 127); |
| } |
| |
| __m256h test_mm256_minmax_ph(__m256h __A, __m256h __B) { |
| // CHECK-LABEL: @test_mm256_minmax_ph( |
| // CHECK: call <16 x half> @llvm.x86.avx10.mask.vminmaxph256( |
| return _mm256_minmax_ph(__A, __B, 127); |
| } |
| |
| __m256h test_mm256_mask_minmax_ph(__m256h __A, __mmask16 __B, __m256h __C, __m256h __D) { |
| // CHECK-LABEL: @test_mm256_mask_minmax_ph( |
| // CHECK: call <16 x half> @llvm.x86.avx10.mask.vminmaxph256( |
| return _mm256_mask_minmax_ph(__A, __B, __C, __D, 127); |
| } |
| |
| __m256h test_mm256_maskz_minmax_ph(__mmask16 __A, __m256h __B, __m256h __C) { |
| // CHECK-LABEL: @test_mm256_maskz_minmax_ph( |
| // CHECK: call <16 x half> @llvm.x86.avx10.mask.vminmaxph256( |
| return _mm256_maskz_minmax_ph(__A, __B, __C, 127); |
| } |
| |
| __m128 test_mm_minmax_ps(__m128 __A, __m128 __B) { |
| // CHECK-LABEL: @test_mm_minmax_ps( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxps128( |
| return _mm_minmax_ps(__A, __B, 127); |
| } |
| |
| __m128 test_mm_mask_minmax_ps(__m128 __A, __mmask8 __B, __m128 __C, __m128 __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_ps( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxps128( |
| return _mm_mask_minmax_ps(__A, __B, __C, __D, 127); |
| } |
| |
| __m128 test_mm_maskz_minmax_ps(__mmask8 __A, __m128 __B, __m128 __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_ps( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxps128( |
| return _mm_maskz_minmax_ps(__A, __B, __C, 127); |
| } |
| |
| __m256 test_mm256_minmax_ps(__m256 __A, __m256 __B) { |
| // CHECK-LABEL: @test_mm256_minmax_ps( |
| // CHECK: call <8 x float> @llvm.x86.avx10.mask.vminmaxps256( |
| return _mm256_minmax_ps(__A, __B, 127); |
| } |
| |
| __m256 test_mm256_mask_minmax_ps(__m256 __A, __mmask8 __B, __m256 __C, __m256 __D) { |
| // CHECK-LABEL: @test_mm256_mask_minmax_ps( |
| // CHECK: call <8 x float> @llvm.x86.avx10.mask.vminmaxps256( |
| return _mm256_mask_minmax_ps(__A, __B, __C, __D, 127); |
| } |
| |
| __m256 test_mm256_maskz_minmax_ps(__mmask8 __A, __m256 __B, __m256 __C) { |
| // CHECK-LABEL: @test_mm256_maskz_minmax_ps( |
| // CHECK: call <8 x float> @llvm.x86.avx10.mask.vminmaxps256( |
| return _mm256_maskz_minmax_ps(__A, __B, __C, 127); |
| } |
| |
| __m128d test_mm_minmax_sd(__m128d __A, __m128d __B) { |
| // CHECK-LABEL: @test_mm_minmax_sd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxsd.round( |
| return _mm_minmax_sd(__A, __B, 127); |
| } |
| |
| __m128d test_mm_mask_minmax_sd(__m128d __A, __mmask8 __B, __m128d __C, __m128d __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_sd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxsd.round( |
| return _mm_mask_minmax_sd(__A, __B, __C, __D, 127); |
| } |
| |
| __m128d test_mm_maskz_minmax_sd(__mmask8 __A, __m128d __B, __m128d __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_sd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxsd.round( |
| return _mm_maskz_minmax_sd(__A, __B, __C, 127); |
| } |
| |
| __m128d test_mm_minmax_round_sd(__m128d __A, __m128d __B) { |
| // CHECK-LABEL: @test_mm_minmax_round_sd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxsd.round( |
| return _mm_minmax_round_sd(__A, __B, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128d test_mm_mask_minmax_round_sd(__m128d __A, __mmask8 __B, __m128d __C, __m128d __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_round_sd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxsd.round( |
| return _mm_mask_minmax_round_sd(__A, __B, __C, __D, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128d test_mm_maskz_minmax_round_sd(__mmask8 __A, __m128d __B, __m128d __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_round_sd( |
| // CHECK: call <2 x double> @llvm.x86.avx10.mask.vminmaxsd.round( |
| return _mm_maskz_minmax_round_sd(__A, __B, __C, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128h test_mm_minmax_sh(__m128h __A, __m128h __B) { |
| // CHECK-LABEL: @test_mm_minmax_sh( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxsh.round( |
| return _mm_minmax_sh(__A, __B, 127); |
| } |
| |
| __m128h test_mm_mask_minmax_sh(__m128h __A, __mmask8 __B, __m128h __C, __m128h __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_sh( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxsh.round( |
| return _mm_mask_minmax_sh(__A, __B, __C, __D, 127); |
| } |
| |
| __m128h test_mm_maskz_minmax_sh(__mmask8 __A, __m128h __B, __m128h __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_sh( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxsh.round( |
| return _mm_maskz_minmax_sh(__A, __B, __C, 127); |
| } |
| |
| __m128h test_mm_minmax_round_sh(__m128h __A, __m128h __B) { |
| // CHECK-LABEL: @test_mm_minmax_round_sh( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxsh.round( |
| return _mm_minmax_round_sh(__A, __B, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128h test_mm_mask_minmax_round_sh(__m128h __A, __mmask8 __B, __m128h __C, __m128h __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_round_sh( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxsh.round( |
| return _mm_mask_minmax_round_sh(__A, __B, __C, __D, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128h test_mm_maskz_minmax_round_sh(__mmask8 __A, __m128h __B, __m128h __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_round_sh( |
| // CHECK: call <8 x half> @llvm.x86.avx10.mask.vminmaxsh.round( |
| return _mm_maskz_minmax_round_sh(__A, __B, __C, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128 test_mm_minmax_ss(__m128 __A, __m128 __B) { |
| // CHECK-LABEL: @test_mm_minmax_ss( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxss.round( |
| return _mm_minmax_ss(__A, __B, 127); |
| } |
| |
| __m128 test_mm_mask_minmax_ss(__m128 __A, __mmask8 __B, __m128 __C, __m128 __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_ss( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxss.round( |
| return _mm_mask_minmax_ss(__A, __B, __C, __D, 127); |
| } |
| |
| __m128 test_mm_maskz_minmax_ss(__mmask8 __A, __m128 __B, __m128 __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_ss( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxss.round( |
| return _mm_maskz_minmax_ss(__A, __B, __C, 127); |
| } |
| |
| __m128 test_mm_minmax_round_ss(__m128 __A, __m128 __B) { |
| // CHECK-LABEL: @test_mm_minmax_round_ss( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxss.round( |
| return _mm_minmax_round_ss(__A, __B, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128 test_mm_mask_minmax_round_ss(__m128 __A, __mmask8 __B, __m128 __C, __m128 __D) { |
| // CHECK-LABEL: @test_mm_mask_minmax_round_ss( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxss.round( |
| return _mm_mask_minmax_round_ss(__A, __B, __C, __D, 127, _MM_FROUND_NO_EXC); |
| } |
| |
| __m128 test_mm_maskz_minmax_round_ss(__mmask8 __A, __m128 __B, __m128 __C) { |
| // CHECK-LABEL: @test_mm_maskz_minmax_round_ss( |
| // CHECK: call <4 x float> @llvm.x86.avx10.mask.vminmaxss.round( |
| return _mm_maskz_minmax_round_ss(__A, __B, __C, 127, _MM_FROUND_NO_EXC); |
| } |
