diff options
| author | bors <bors@rust-lang.org> | 2018-10-20 22:23:36 +0000 |
|---|---|---|
| committer | bors <bors@rust-lang.org> | 2018-10-20 22:23:36 +0000 |
| commit | d5418764ada3ce7b308de7a0e6e260548a635afc (patch) | |
| tree | b3fa56e507a8d1a894e35e9a00a70c5ce73e0f67 /src/test | |
| parent | 155510e377ae2a8d8ee0dad1a5f809c9062a5526 (diff) | |
| parent | f2848a010adf22d43fd713975b4945402d585554 (diff) | |
Auto merge of #55230 - Manishearth:rollup, r=Manishearth
Rollup of 5 pull requests Successful merges: - #55156 (Fixed: Multiple errors on single typo in match pattern) - #55189 (update books for the next release) - #55193 (make asm diagnostic instruction optional) - #55203 (Write an initial version of the `program_clauses` callback) - #55213 (ignore target folders) Failed merges: r? @ghost
Diffstat (limited to 'src/test')
4 files changed, 100 insertions, 0 deletions
diff --git a/src/test/run-make/simd-argument-promotion-thwarted/Makefile b/src/test/run-make/simd-argument-promotion-thwarted/Makefile new file mode 100644 index 00000000000..3095432d0fe --- /dev/null +++ b/src/test/run-make/simd-argument-promotion-thwarted/Makefile @@ -0,0 +1,13 @@ +-include ../../run-make-fulldeps/tools.mk + +ifeq ($(TARGET),x86_64-unknown-linux-gnu) +all: + $(RUSTC) t1.rs -C opt-level=3 + $(TMPDIR)/t1 + $(RUSTC) t2.rs -C opt-level=3 + $(TMPDIR)/t2 + $(RUSTC) t3.rs -C opt-level=3 + $(TMPDIR)/t3 +else +all: +endif diff --git a/src/test/run-make/simd-argument-promotion-thwarted/t1.rs b/src/test/run-make/simd-argument-promotion-thwarted/t1.rs new file mode 100644 index 00000000000..cb4a3dd7d4a --- /dev/null +++ b/src/test/run-make/simd-argument-promotion-thwarted/t1.rs @@ -0,0 +1,21 @@ +use std::arch::x86_64; + +fn main() { + if !is_x86_feature_detected!("avx2") { + return println!("AVX2 is not supported on this machine/build."); + } + let load_bytes: [u8; 32] = [0x0f; 32]; + let lb_ptr = load_bytes.as_ptr(); + let reg_load = unsafe { + x86_64::_mm256_loadu_si256( + lb_ptr as *const x86_64::__m256i + ) + }; + println!("{:?}", reg_load); + let mut store_bytes: [u8; 32] = [0; 32]; + let sb_ptr = store_bytes.as_mut_ptr(); + unsafe { + x86_64::_mm256_storeu_si256(sb_ptr as *mut x86_64::__m256i, reg_load); + } + assert_eq!(load_bytes, store_bytes); +} diff --git a/src/test/run-make/simd-argument-promotion-thwarted/t2.rs b/src/test/run-make/simd-argument-promotion-thwarted/t2.rs new file mode 100644 index 00000000000..0e42b82a223 --- /dev/null +++ b/src/test/run-make/simd-argument-promotion-thwarted/t2.rs @@ -0,0 +1,14 @@ +use std::arch::x86_64::*; + +fn main() { + if !is_x86_feature_detected!("avx") { + return println!("AVX is not supported on this machine/build."); + } + unsafe { + let f = _mm256_set_pd(2.0, 2.0, 2.0, 2.0); + let r = _mm256_mul_pd(f, f); + + union A { a: __m256d, b: [f64; 4] } + assert_eq!(A { a: r }.b, [4.0, 4.0, 4.0, 4.0]); + } +} diff --git a/src/test/run-make/simd-argument-promotion-thwarted/t3.rs b/src/test/run-make/simd-argument-promotion-thwarted/t3.rs new file mode 100644 index 00000000000..10062ab3e46 --- /dev/null +++ b/src/test/run-make/simd-argument-promotion-thwarted/t3.rs @@ -0,0 +1,52 @@ +use std::arch::x86_64::*; + +#[target_feature(enable = "avx")] +unsafe fn avx_mul(a: __m256, b: __m256) -> __m256 { + _mm256_mul_ps(a, b) +} + +#[target_feature(enable = "avx")] +unsafe fn avx_store(p: *mut f32, a: __m256) { + _mm256_storeu_ps(p, a) +} + +#[target_feature(enable = "avx")] +unsafe fn avx_setr(a: f32, b: f32, c: f32, d: f32, e: f32, f: f32, g: f32, h: f32) -> __m256 { + _mm256_setr_ps(a, b, c, d, e, f, g, h) +} + +#[target_feature(enable = "avx")] +unsafe fn avx_set1(a: f32) -> __m256 { + _mm256_set1_ps(a) +} + +struct Avx(__m256); + +fn mul(a: Avx, b: Avx) -> Avx { + unsafe { Avx(avx_mul(a.0, b.0)) } +} + +fn set1(a: f32) -> Avx { + unsafe { Avx(avx_set1(a)) } +} + +fn setr(a: f32, b: f32, c: f32, d: f32, e: f32, f: f32, g: f32, h: f32) -> Avx { + unsafe { Avx(avx_setr(a, b, c, d, e, f, g, h)) } +} + +unsafe fn store(p: *mut f32, a: Avx) { + avx_store(p, a.0); +} + +fn main() { + if !is_x86_feature_detected!("avx") { + return println!("AVX is not supported on this machine/build."); + } + let mut result = [0.0f32; 8]; + let a = mul(setr(0.0, 1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0), set1(0.25)); + unsafe { + store(result.as_mut_ptr(), a); + } + + assert_eq!(result, [0.0, 0.25, 0.5, 0.75, 1.0, 1.25, 1.50, 1.75]); +} |
