user0/rust
1
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity Actions

Add vld1q_dup_f32 (#897)

Browse source
This commit is contained in:
Jeff Muizelaar 2020-09-08 09:39:56 -04:00 • committed by GitHub
parent e8a9e43f93
commit 78c5f04228
No known key found for this signature in database
GPG key ID: 4AEE18F83AFDEB23
1 changed files with 20 additions and 0 deletions
Download patch file Download diff file Expand all files Collapse all files

20
library/stdarch/crates/core_arch/src/arm/neon/mod.rs
View file

@ -1779,6 +1779,18 @@ pub unsafe fn vld1q_f32(addr: *const f32) -> float32x4_t {
vld1q_v4f32(addr as *const u8, 4)
}
/// Load one single-element structure and Replicate to all lanes (of one register).
#[inline]
#[target_feature(enable = "neon")]
#[cfg_attr(target_arch = "arm", target_feature(enable = "v7"))]
#[cfg_attr(all(test, target_arch = "arm"), assert_instr("vld1.32"))]
#[cfg_attr(all(test, target_arch = "aarch64"), assert_instr(ld1r))]
pub unsafe fn vld1q_dup_f32(addr: *const f32) -> float32x4_t {
use crate::core_arch::simd::f32x4;
let v = *addr;
transmute(f32x4::new(v, v, v, v))
}
#[cfg(test)]
mod tests {
use super::*;
@ -1814,6 +1826,14 @@ mod tests {
assert_eq!(r, e);
}
#[simd_test(enable = "neon")]
unsafe fn test_vld1q_dup_f32() {
let e = f32x4::new(1., 1., 1., 1.);
let f = [1., 2., 3., 4.];
let r: f32x4 = transmute(vld1q_dup_f32(f.as_ptr()));
assert_eq!(r, e);
}
#[simd_test(enable = "neon")]
unsafe fn test_vget_lane_u8() {
let v = i8x8::new(1, 2, 3, 4, 5, 6, 7, 8);