Skip to content

Remove workaround for issue that has been fixed since Rust 1.61. #125

New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Merged
hkratz merged 1 commit into from
Jun 14, 2026
Merged

Remove workaround for issue that has been fixed since Rust 1.61. #125

Changes from all commits
Commits
Show all changes
1 commit
Select commit
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
14 changes: 1 addition & 13 deletions src/implementation/aarch64/neon.rs
View file
Open in desktop
Original file line number Diff line number Diff line change
Expand Up @@ -82,19 +82,7 @@ impl SimdU8Value {

#[inline]
unsafe fn load_from(ptr: *const u8) -> Self {
// WORKAROUND for https://github.com/rust-lang/stdarch/issues/1148
// The vld1q_u8 intrinsic is currently broken, it treats it as individual
// byte loads so the compiler sometimes decides it is a better to load
// individual bytes to "optimize" a subsequent SIMD shuffle
//
// This code forces a full 128-bit load.
let mut dst = core::mem::MaybeUninit::<uint8x16_t>::uninit();
core::ptr::copy_nonoverlapping(
ptr.cast::<u8>(),
dst.as_mut_ptr().cast::<u8>(),
core::mem::size_of::<uint8x16_t>(),
);
Self::from(dst.assume_init())
Self::from(vld1q_u8(ptr))
}

#[inline]
Expand Down
Loading