Add tracking issue for ARM NEON instructions
This commit is contained in:
Amanieu d'Antras
parent
ed25ca9875
commit
1dcafa2caf
5 changed files with 3835 additions and 6 deletions
|
|
@ -125,6 +125,7 @@ extern "unadjusted" {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_s8(ptr: *const i8) -> int8x8_t {
|
||||
vld1_v8i8(ptr as *const i8, align_of::<i8>() as i32)
|
||||
}
|
||||
|
|
@ -133,6 +134,7 @@ pub unsafe fn vld1_s8(ptr: *const i8) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_s8(ptr: *const i8) -> int8x16_t {
|
||||
vld1q_v16i8(ptr as *const i8, align_of::<i8>() as i32)
|
||||
}
|
||||
|
|
@ -141,6 +143,7 @@ pub unsafe fn vld1q_s8(ptr: *const i8) -> int8x16_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_s16(ptr: *const i16) -> int16x4_t {
|
||||
vld1_v4i16(ptr as *const i8, align_of::<i16>() as i32)
|
||||
}
|
||||
|
|
@ -149,6 +152,7 @@ pub unsafe fn vld1_s16(ptr: *const i16) -> int16x4_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_s16(ptr: *const i16) -> int16x8_t {
|
||||
vld1q_v8i16(ptr as *const i8, align_of::<i16>() as i32)
|
||||
}
|
||||
|
|
@ -157,6 +161,7 @@ pub unsafe fn vld1q_s16(ptr: *const i16) -> int16x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vldr))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_s32(ptr: *const i32) -> int32x2_t {
|
||||
vld1_v2i32(ptr as *const i8, align_of::<i32>() as i32)
|
||||
}
|
||||
|
|
@ -165,6 +170,7 @@ pub unsafe fn vld1_s32(ptr: *const i32) -> int32x2_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_s32(ptr: *const i32) -> int32x4_t {
|
||||
vld1q_v4i32(ptr as *const i8, align_of::<i32>() as i32)
|
||||
}
|
||||
|
|
@ -173,6 +179,7 @@ pub unsafe fn vld1q_s32(ptr: *const i32) -> int32x4_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vldr))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_s64(ptr: *const i64) -> int64x1_t {
|
||||
vld1_v1i64(ptr as *const i8, align_of::<i64>() as i32)
|
||||
}
|
||||
|
|
@ -181,6 +188,7 @@ pub unsafe fn vld1_s64(ptr: *const i64) -> int64x1_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_s64(ptr: *const i64) -> int64x2_t {
|
||||
vld1q_v2i64(ptr as *const i8, align_of::<i64>() as i32)
|
||||
}
|
||||
|
|
@ -189,6 +197,7 @@ pub unsafe fn vld1q_s64(ptr: *const i64) -> int64x2_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_u8(ptr: *const u8) -> uint8x8_t {
|
||||
transmute(vld1_v8i8(ptr as *const i8, align_of::<u8>() as i32))
|
||||
}
|
||||
|
|
@ -197,6 +206,7 @@ pub unsafe fn vld1_u8(ptr: *const u8) -> uint8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_u8(ptr: *const u8) -> uint8x16_t {
|
||||
transmute(vld1q_v16i8(ptr as *const i8, align_of::<u8>() as i32))
|
||||
}
|
||||
|
|
@ -205,6 +215,7 @@ pub unsafe fn vld1q_u8(ptr: *const u8) -> uint8x16_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_u16(ptr: *const u16) -> uint16x4_t {
|
||||
transmute(vld1_v4i16(ptr as *const i8, align_of::<u16>() as i32))
|
||||
}
|
||||
|
|
@ -213,6 +224,7 @@ pub unsafe fn vld1_u16(ptr: *const u16) -> uint16x4_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_u16(ptr: *const u16) -> uint16x8_t {
|
||||
transmute(vld1q_v8i16(ptr as *const i8, align_of::<u16>() as i32))
|
||||
}
|
||||
|
|
@ -221,6 +233,7 @@ pub unsafe fn vld1q_u16(ptr: *const u16) -> uint16x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vldr))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_u32(ptr: *const u32) -> uint32x2_t {
|
||||
transmute(vld1_v2i32(ptr as *const i8, align_of::<u32>() as i32))
|
||||
}
|
||||
|
|
@ -229,6 +242,7 @@ pub unsafe fn vld1_u32(ptr: *const u32) -> uint32x2_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_u32(ptr: *const u32) -> uint32x4_t {
|
||||
transmute(vld1q_v4i32(ptr as *const i8, align_of::<u32>() as i32))
|
||||
}
|
||||
|
|
@ -237,6 +251,7 @@ pub unsafe fn vld1q_u32(ptr: *const u32) -> uint32x4_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vldr))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_u64(ptr: *const u64) -> uint64x1_t {
|
||||
transmute(vld1_v1i64(ptr as *const i8, align_of::<u64>() as i32))
|
||||
}
|
||||
|
|
@ -245,6 +260,7 @@ pub unsafe fn vld1_u64(ptr: *const u64) -> uint64x1_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_u64(ptr: *const u64) -> uint64x2_t {
|
||||
transmute(vld1q_v2i64(ptr as *const i8, align_of::<u64>() as i32))
|
||||
}
|
||||
|
|
@ -253,6 +269,7 @@ pub unsafe fn vld1q_u64(ptr: *const u64) -> uint64x2_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_p8(ptr: *const p8) -> poly8x8_t {
|
||||
transmute(vld1_v8i8(ptr as *const i8, align_of::<p8>() as i32))
|
||||
}
|
||||
|
|
@ -261,6 +278,7 @@ pub unsafe fn vld1_p8(ptr: *const p8) -> poly8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_p8(ptr: *const p8) -> poly8x16_t {
|
||||
transmute(vld1q_v16i8(ptr as *const i8, align_of::<p8>() as i32))
|
||||
}
|
||||
|
|
@ -269,6 +287,7 @@ pub unsafe fn vld1q_p8(ptr: *const p8) -> poly8x16_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_p16(ptr: *const p16) -> poly16x4_t {
|
||||
transmute(vld1_v4i16(ptr as *const i8, align_of::<p16>() as i32))
|
||||
}
|
||||
|
|
@ -277,6 +296,7 @@ pub unsafe fn vld1_p16(ptr: *const p16) -> poly16x4_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_p16(ptr: *const p16) -> poly16x8_t {
|
||||
transmute(vld1q_v8i16(ptr as *const i8, align_of::<p16>() as i32))
|
||||
}
|
||||
|
|
@ -287,6 +307,7 @@ pub unsafe fn vld1q_p16(ptr: *const p16) -> poly16x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,aes")]
|
||||
#[cfg_attr(test, assert_instr(vldr))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_p64(ptr: *const p64) -> poly64x1_t {
|
||||
transmute(vld1_v1i64(ptr as *const i8, align_of::<p64>() as i32))
|
||||
}
|
||||
|
|
@ -297,6 +318,7 @@ pub unsafe fn vld1_p64(ptr: *const p64) -> poly64x1_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,aes")]
|
||||
#[cfg_attr(test, assert_instr("vld1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_p64(ptr: *const p64) -> poly64x2_t {
|
||||
transmute(vld1q_v2i64(ptr as *const i8, align_of::<p64>() as i32))
|
||||
}
|
||||
|
|
@ -305,6 +327,7 @@ pub unsafe fn vld1q_p64(ptr: *const p64) -> poly64x2_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vldr))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1_f32(ptr: *const f32) -> float32x2_t {
|
||||
vld1_v2f32(ptr as *const i8, align_of::<f32>() as i32)
|
||||
}
|
||||
|
|
@ -313,6 +336,7 @@ pub unsafe fn vld1_f32(ptr: *const f32) -> float32x2_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vld1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vld1q_f32(ptr: *const f32) -> float32x4_t {
|
||||
vld1q_v4f32(ptr as *const i8, align_of::<f32>() as i32)
|
||||
}
|
||||
|
|
@ -321,6 +345,7 @@ pub unsafe fn vld1q_f32(ptr: *const f32) -> float32x4_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_s8(ptr: *mut i8, a: int8x8_t) {
|
||||
vst1_v8i8(ptr as *const i8, a, align_of::<i8>() as i32)
|
||||
}
|
||||
|
|
@ -329,6 +354,7 @@ pub unsafe fn vst1_s8(ptr: *mut i8, a: int8x8_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_s8(ptr: *mut i8, a: int8x16_t) {
|
||||
vst1q_v16i8(ptr as *const i8, a, align_of::<i8>() as i32)
|
||||
}
|
||||
|
|
@ -337,6 +363,7 @@ pub unsafe fn vst1q_s8(ptr: *mut i8, a: int8x16_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_s16(ptr: *mut i16, a: int16x4_t) {
|
||||
vst1_v4i16(ptr as *const i8, a, align_of::<i16>() as i32)
|
||||
}
|
||||
|
|
@ -345,6 +372,7 @@ pub unsafe fn vst1_s16(ptr: *mut i16, a: int16x4_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_s16(ptr: *mut i16, a: int16x8_t) {
|
||||
vst1q_v8i16(ptr as *const i8, a, align_of::<i16>() as i32)
|
||||
}
|
||||
|
|
@ -353,6 +381,7 @@ pub unsafe fn vst1q_s16(ptr: *mut i16, a: int16x8_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_s32(ptr: *mut i32, a: int32x2_t) {
|
||||
vst1_v2i32(ptr as *const i8, a, align_of::<i32>() as i32)
|
||||
}
|
||||
|
|
@ -361,6 +390,7 @@ pub unsafe fn vst1_s32(ptr: *mut i32, a: int32x2_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_s32(ptr: *mut i32, a: int32x4_t) {
|
||||
vst1q_v4i32(ptr as *const i8, a, align_of::<i32>() as i32)
|
||||
}
|
||||
|
|
@ -369,6 +399,7 @@ pub unsafe fn vst1q_s32(ptr: *mut i32, a: int32x4_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_s64(ptr: *mut i64, a: int64x1_t) {
|
||||
vst1_v1i64(ptr as *const i8, a, align_of::<i64>() as i32)
|
||||
}
|
||||
|
|
@ -377,6 +408,7 @@ pub unsafe fn vst1_s64(ptr: *mut i64, a: int64x1_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_s64(ptr: *mut i64, a: int64x2_t) {
|
||||
vst1q_v2i64(ptr as *const i8, a, align_of::<i64>() as i32)
|
||||
}
|
||||
|
|
@ -385,6 +417,7 @@ pub unsafe fn vst1q_s64(ptr: *mut i64, a: int64x2_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_u8(ptr: *mut u8, a: uint8x8_t) {
|
||||
vst1_v8i8(ptr as *const i8, transmute(a), align_of::<u8>() as i32)
|
||||
}
|
||||
|
|
@ -393,6 +426,7 @@ pub unsafe fn vst1_u8(ptr: *mut u8, a: uint8x8_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_u8(ptr: *mut u8, a: uint8x16_t) {
|
||||
vst1q_v16i8(ptr as *const i8, transmute(a), align_of::<u8>() as i32)
|
||||
}
|
||||
|
|
@ -401,6 +435,7 @@ pub unsafe fn vst1q_u8(ptr: *mut u8, a: uint8x16_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_u16(ptr: *mut u16, a: uint16x4_t) {
|
||||
vst1_v4i16(ptr as *const i8, transmute(a), align_of::<u16>() as i32)
|
||||
}
|
||||
|
|
@ -409,6 +444,7 @@ pub unsafe fn vst1_u16(ptr: *mut u16, a: uint16x4_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_u16(ptr: *mut u16, a: uint16x8_t) {
|
||||
vst1q_v8i16(ptr as *const i8, transmute(a), align_of::<u16>() as i32)
|
||||
}
|
||||
|
|
@ -417,6 +453,7 @@ pub unsafe fn vst1q_u16(ptr: *mut u16, a: uint16x8_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_u32(ptr: *mut u32, a: uint32x2_t) {
|
||||
vst1_v2i32(ptr as *const i8, transmute(a), align_of::<u32>() as i32)
|
||||
}
|
||||
|
|
@ -425,6 +462,7 @@ pub unsafe fn vst1_u32(ptr: *mut u32, a: uint32x2_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_u32(ptr: *mut u32, a: uint32x4_t) {
|
||||
vst1q_v4i32(ptr as *const i8, transmute(a), align_of::<u32>() as i32)
|
||||
}
|
||||
|
|
@ -433,6 +471,7 @@ pub unsafe fn vst1q_u32(ptr: *mut u32, a: uint32x4_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_u64(ptr: *mut u64, a: uint64x1_t) {
|
||||
vst1_v1i64(ptr as *const i8, transmute(a), align_of::<u64>() as i32)
|
||||
}
|
||||
|
|
@ -441,6 +480,7 @@ pub unsafe fn vst1_u64(ptr: *mut u64, a: uint64x1_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_u64(ptr: *mut u64, a: uint64x2_t) {
|
||||
vst1q_v2i64(ptr as *const i8, transmute(a), align_of::<u64>() as i32)
|
||||
}
|
||||
|
|
@ -449,6 +489,7 @@ pub unsafe fn vst1q_u64(ptr: *mut u64, a: uint64x2_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_p8(ptr: *mut p8, a: poly8x8_t) {
|
||||
vst1_v8i8(ptr as *const i8, transmute(a), align_of::<p8>() as i32)
|
||||
}
|
||||
|
|
@ -457,6 +498,7 @@ pub unsafe fn vst1_p8(ptr: *mut p8, a: poly8x8_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.8"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_p8(ptr: *mut p8, a: poly8x16_t) {
|
||||
vst1q_v16i8(ptr as *const i8, transmute(a), align_of::<p8>() as i32)
|
||||
}
|
||||
|
|
@ -465,6 +507,7 @@ pub unsafe fn vst1q_p8(ptr: *mut p8, a: poly8x16_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_p16(ptr: *mut p16, a: poly16x4_t) {
|
||||
vst1_v4i16(ptr as *const i8, transmute(a), align_of::<p16>() as i32)
|
||||
}
|
||||
|
|
@ -473,6 +516,7 @@ pub unsafe fn vst1_p16(ptr: *mut p16, a: poly16x4_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.16"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_p16(ptr: *mut p16, a: poly16x8_t) {
|
||||
vst1q_v8i16(ptr as *const i8, transmute(a), align_of::<p8>() as i32)
|
||||
}
|
||||
|
|
@ -483,6 +527,7 @@ pub unsafe fn vst1q_p16(ptr: *mut p16, a: poly16x8_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,aes,v8")]
|
||||
#[cfg_attr(test, assert_instr("vst1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_p64(ptr: *mut p64, a: poly64x1_t) {
|
||||
vst1_v1i64(ptr as *const i8, transmute(a), align_of::<p64>() as i32)
|
||||
}
|
||||
|
|
@ -493,6 +538,7 @@ pub unsafe fn vst1_p64(ptr: *mut p64, a: poly64x1_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,aes,v8")]
|
||||
#[cfg_attr(test, assert_instr("vst1.64"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_p64(ptr: *mut p64, a: poly64x2_t) {
|
||||
vst1q_v2i64(ptr as *const i8, transmute(a), align_of::<p64>() as i32)
|
||||
}
|
||||
|
|
@ -501,6 +547,7 @@ pub unsafe fn vst1q_p64(ptr: *mut p64, a: poly64x2_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1_f32(ptr: *mut f32, a: float32x2_t) {
|
||||
vst1_v2f32(ptr as *const i8, a, align_of::<f32>() as i32)
|
||||
}
|
||||
|
|
@ -509,6 +556,7 @@ pub unsafe fn vst1_f32(ptr: *mut f32, a: float32x2_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vst1.32"))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vst1q_f32(ptr: *mut f32, a: float32x4_t) {
|
||||
vst1q_v4f32(ptr as *const i8, a, align_of::<f32>() as i32)
|
||||
}
|
||||
|
|
@ -517,6 +565,7 @@ pub unsafe fn vst1q_f32(ptr: *mut f32, a: float32x4_t) {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl1_s8(a: int8x8_t, b: int8x8_t) -> int8x8_t {
|
||||
vtbl1(a, b)
|
||||
}
|
||||
|
|
@ -525,6 +574,7 @@ pub unsafe fn vtbl1_s8(a: int8x8_t, b: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl1_u8(a: uint8x8_t, b: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbl1(transmute(a), transmute(b)))
|
||||
}
|
||||
|
|
@ -533,6 +583,7 @@ pub unsafe fn vtbl1_u8(a: uint8x8_t, b: uint8x8_t) -> uint8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl1_p8(a: poly8x8_t, b: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbl1(transmute(a), transmute(b)))
|
||||
}
|
||||
|
|
@ -541,6 +592,7 @@ pub unsafe fn vtbl1_p8(a: poly8x8_t, b: uint8x8_t) -> poly8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl2_s8(a: int8x8x2_t, b: int8x8_t) -> int8x8_t {
|
||||
vtbl2(a.0, a.1, b)
|
||||
}
|
||||
|
|
@ -549,6 +601,7 @@ pub unsafe fn vtbl2_s8(a: int8x8x2_t, b: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl2_u8(a: uint8x8x2_t, b: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbl2(transmute(a.0), transmute(a.1), transmute(b)))
|
||||
}
|
||||
|
|
@ -557,6 +610,7 @@ pub unsafe fn vtbl2_u8(a: uint8x8x2_t, b: uint8x8_t) -> uint8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl2_p8(a: poly8x8x2_t, b: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbl2(transmute(a.0), transmute(a.1), transmute(b)))
|
||||
}
|
||||
|
|
@ -565,6 +619,7 @@ pub unsafe fn vtbl2_p8(a: poly8x8x2_t, b: uint8x8_t) -> poly8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl3_s8(a: int8x8x3_t, b: int8x8_t) -> int8x8_t {
|
||||
vtbl3(a.0, a.1, a.2, b)
|
||||
}
|
||||
|
|
@ -573,6 +628,7 @@ pub unsafe fn vtbl3_s8(a: int8x8x3_t, b: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl3_u8(a: uint8x8x3_t, b: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbl3(
|
||||
transmute(a.0),
|
||||
|
|
@ -586,6 +642,7 @@ pub unsafe fn vtbl3_u8(a: uint8x8x3_t, b: uint8x8_t) -> uint8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl3_p8(a: poly8x8x3_t, b: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbl3(
|
||||
transmute(a.0),
|
||||
|
|
@ -599,6 +656,7 @@ pub unsafe fn vtbl3_p8(a: poly8x8x3_t, b: uint8x8_t) -> poly8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl4_s8(a: int8x8x4_t, b: int8x8_t) -> int8x8_t {
|
||||
vtbl4(a.0, a.1, a.2, a.3, b)
|
||||
}
|
||||
|
|
@ -607,6 +665,7 @@ pub unsafe fn vtbl4_s8(a: int8x8x4_t, b: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl4_u8(a: uint8x8x4_t, b: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbl4(
|
||||
transmute(a.0),
|
||||
|
|
@ -621,6 +680,7 @@ pub unsafe fn vtbl4_u8(a: uint8x8x4_t, b: uint8x8_t) -> uint8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbl))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbl4_p8(a: poly8x8x4_t, b: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbl4(
|
||||
transmute(a.0),
|
||||
|
|
@ -635,6 +695,7 @@ pub unsafe fn vtbl4_p8(a: poly8x8x4_t, b: uint8x8_t) -> poly8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx1_s8(a: int8x8_t, b: int8x8_t, c: int8x8_t) -> int8x8_t {
|
||||
vtbx1(a, b, c)
|
||||
}
|
||||
|
|
@ -643,6 +704,7 @@ pub unsafe fn vtbx1_s8(a: int8x8_t, b: int8x8_t, c: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx1_u8(a: uint8x8_t, b: uint8x8_t, c: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbx1(transmute(a), transmute(b), transmute(c)))
|
||||
}
|
||||
|
|
@ -651,6 +713,7 @@ pub unsafe fn vtbx1_u8(a: uint8x8_t, b: uint8x8_t, c: uint8x8_t) -> uint8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx1_p8(a: poly8x8_t, b: poly8x8_t, c: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbx1(transmute(a), transmute(b), transmute(c)))
|
||||
}
|
||||
|
|
@ -659,6 +722,7 @@ pub unsafe fn vtbx1_p8(a: poly8x8_t, b: poly8x8_t, c: uint8x8_t) -> poly8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx2_s8(a: int8x8_t, b: int8x8x2_t, c: int8x8_t) -> int8x8_t {
|
||||
vtbx2(a, b.0, b.1, c)
|
||||
}
|
||||
|
|
@ -667,6 +731,7 @@ pub unsafe fn vtbx2_s8(a: int8x8_t, b: int8x8x2_t, c: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx2_u8(a: uint8x8_t, b: uint8x8x2_t, c: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbx2(
|
||||
transmute(a),
|
||||
|
|
@ -680,6 +745,7 @@ pub unsafe fn vtbx2_u8(a: uint8x8_t, b: uint8x8x2_t, c: uint8x8_t) -> uint8x8_t
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx2_p8(a: poly8x8_t, b: poly8x8x2_t, c: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbx2(
|
||||
transmute(a),
|
||||
|
|
@ -693,6 +759,7 @@ pub unsafe fn vtbx2_p8(a: poly8x8_t, b: poly8x8x2_t, c: uint8x8_t) -> poly8x8_t
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx3_s8(a: int8x8_t, b: int8x8x3_t, c: int8x8_t) -> int8x8_t {
|
||||
vtbx3(a, b.0, b.1, b.2, c)
|
||||
}
|
||||
|
|
@ -701,6 +768,7 @@ pub unsafe fn vtbx3_s8(a: int8x8_t, b: int8x8x3_t, c: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx3_u8(a: uint8x8_t, b: uint8x8x3_t, c: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbx3(
|
||||
transmute(a),
|
||||
|
|
@ -715,6 +783,7 @@ pub unsafe fn vtbx3_u8(a: uint8x8_t, b: uint8x8x3_t, c: uint8x8_t) -> uint8x8_t
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx3_p8(a: poly8x8_t, b: poly8x8x3_t, c: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbx3(
|
||||
transmute(a),
|
||||
|
|
@ -729,6 +798,7 @@ pub unsafe fn vtbx3_p8(a: poly8x8_t, b: poly8x8x3_t, c: uint8x8_t) -> poly8x8_t
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx4_s8(a: int8x8_t, b: int8x8x4_t, c: int8x8_t) -> int8x8_t {
|
||||
vtbx4(a, b.0, b.1, b.2, b.3, c)
|
||||
}
|
||||
|
|
@ -737,6 +807,7 @@ pub unsafe fn vtbx4_s8(a: int8x8_t, b: int8x8x4_t, c: int8x8_t) -> int8x8_t {
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx4_u8(a: uint8x8_t, b: uint8x8x4_t, c: uint8x8_t) -> uint8x8_t {
|
||||
transmute(vtbx4(
|
||||
transmute(a),
|
||||
|
|
@ -752,6 +823,7 @@ pub unsafe fn vtbx4_u8(a: uint8x8_t, b: uint8x8x4_t, c: uint8x8_t) -> uint8x8_t
|
|||
#[inline]
|
||||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr(vtbx))]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vtbx4_p8(a: poly8x8_t, b: poly8x8x4_t, c: uint8x8_t) -> poly8x8_t {
|
||||
transmute(vtbx4(
|
||||
transmute(a),
|
||||
|
|
@ -768,6 +840,7 @@ pub unsafe fn vtbx4_p8(a: poly8x8_t, b: poly8x8x4_t, c: uint8x8_t) -> poly8x8_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_s8<const N: i32>(a: int8x8_t, b: int8x8_t) -> int8x8_t {
|
||||
static_assert_uimm_bits!(N, 3);
|
||||
let n = N as i8;
|
||||
|
|
@ -778,6 +851,7 @@ pub unsafe fn vsli_n_s8<const N: i32>(a: int8x8_t, b: int8x8_t) -> int8x8_t {
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_s8<const N: i32>(a: int8x16_t, b: int8x16_t) -> int8x16_t {
|
||||
static_assert_uimm_bits!(N, 3);
|
||||
let n = N as i8;
|
||||
|
|
@ -792,6 +866,7 @@ pub unsafe fn vsliq_n_s8<const N: i32>(a: int8x16_t, b: int8x16_t) -> int8x16_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_s16<const N: i32>(a: int16x4_t, b: int16x4_t) -> int16x4_t {
|
||||
static_assert_uimm_bits!(N, 4);
|
||||
let n = N as i16;
|
||||
|
|
@ -802,6 +877,7 @@ pub unsafe fn vsli_n_s16<const N: i32>(a: int16x4_t, b: int16x4_t) -> int16x4_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_s16<const N: i32>(a: int16x8_t, b: int16x8_t) -> int16x8_t {
|
||||
static_assert_uimm_bits!(N, 4);
|
||||
let n = N as i16;
|
||||
|
|
@ -812,6 +888,7 @@ pub unsafe fn vsliq_n_s16<const N: i32>(a: int16x8_t, b: int16x8_t) -> int16x8_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_s32<const N: i32>(a: int32x2_t, b: int32x2_t) -> int32x2_t {
|
||||
static_assert!(N >= 0 && N <= 31);
|
||||
vshiftins_v2i32(a, b, int32x2_t(N, N))
|
||||
|
|
@ -821,6 +898,7 @@ pub unsafe fn vsli_n_s32<const N: i32>(a: int32x2_t, b: int32x2_t) -> int32x2_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_s32<const N: i32>(a: int32x4_t, b: int32x4_t) -> int32x4_t {
|
||||
static_assert!(N >= 0 && N <= 31);
|
||||
vshiftins_v4i32(a, b, int32x4_t(N, N, N, N))
|
||||
|
|
@ -830,6 +908,7 @@ pub unsafe fn vsliq_n_s32<const N: i32>(a: int32x4_t, b: int32x4_t) -> int32x4_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_s64<const N: i32>(a: int64x1_t, b: int64x1_t) -> int64x1_t {
|
||||
static_assert!(0 <= N && N <= 63);
|
||||
vshiftins_v1i64(a, b, int64x1_t(N as i64))
|
||||
|
|
@ -839,6 +918,7 @@ pub unsafe fn vsli_n_s64<const N: i32>(a: int64x1_t, b: int64x1_t) -> int64x1_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_s64<const N: i32>(a: int64x2_t, b: int64x2_t) -> int64x2_t {
|
||||
static_assert!(0 <= N && N <= 63);
|
||||
vshiftins_v2i64(a, b, int64x2_t(N as i64, N as i64))
|
||||
|
|
@ -848,6 +928,7 @@ pub unsafe fn vsliq_n_s64<const N: i32>(a: int64x2_t, b: int64x2_t) -> int64x2_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_u8<const N: i32>(a: uint8x8_t, b: uint8x8_t) -> uint8x8_t {
|
||||
static_assert_uimm_bits!(N, 3);
|
||||
let n = N as i8;
|
||||
|
|
@ -862,6 +943,7 @@ pub unsafe fn vsli_n_u8<const N: i32>(a: uint8x8_t, b: uint8x8_t) -> uint8x8_t {
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_u8<const N: i32>(a: uint8x16_t, b: uint8x16_t) -> uint8x16_t {
|
||||
static_assert_uimm_bits!(N, 3);
|
||||
let n = N as i8;
|
||||
|
|
@ -876,6 +958,7 @@ pub unsafe fn vsliq_n_u8<const N: i32>(a: uint8x16_t, b: uint8x16_t) -> uint8x16
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_u16<const N: i32>(a: uint16x4_t, b: uint16x4_t) -> uint16x4_t {
|
||||
static_assert_uimm_bits!(N, 4);
|
||||
let n = N as i16;
|
||||
|
|
@ -890,6 +973,7 @@ pub unsafe fn vsli_n_u16<const N: i32>(a: uint16x4_t, b: uint16x4_t) -> uint16x4
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_u16<const N: i32>(a: uint16x8_t, b: uint16x8_t) -> uint16x8_t {
|
||||
static_assert_uimm_bits!(N, 4);
|
||||
let n = N as i16;
|
||||
|
|
@ -904,6 +988,7 @@ pub unsafe fn vsliq_n_u16<const N: i32>(a: uint16x8_t, b: uint16x8_t) -> uint16x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_u32<const N: i32>(a: uint32x2_t, b: uint32x2_t) -> uint32x2_t {
|
||||
static_assert!(N >= 0 && N <= 31);
|
||||
transmute(vshiftins_v2i32(transmute(a), transmute(b), int32x2_t(N, N)))
|
||||
|
|
@ -913,6 +998,7 @@ pub unsafe fn vsli_n_u32<const N: i32>(a: uint32x2_t, b: uint32x2_t) -> uint32x2
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_u32<const N: i32>(a: uint32x4_t, b: uint32x4_t) -> uint32x4_t {
|
||||
static_assert!(N >= 0 && N <= 31);
|
||||
transmute(vshiftins_v4i32(
|
||||
|
|
@ -926,6 +1012,7 @@ pub unsafe fn vsliq_n_u32<const N: i32>(a: uint32x4_t, b: uint32x4_t) -> uint32x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_u64<const N: i32>(a: uint64x1_t, b: uint64x1_t) -> uint64x1_t {
|
||||
static_assert!(0 <= N && N <= 63);
|
||||
transmute(vshiftins_v1i64(
|
||||
|
|
@ -939,6 +1026,7 @@ pub unsafe fn vsli_n_u64<const N: i32>(a: uint64x1_t, b: uint64x1_t) -> uint64x1
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_u64<const N: i32>(a: uint64x2_t, b: uint64x2_t) -> uint64x2_t {
|
||||
static_assert!(0 <= N && N <= 63);
|
||||
transmute(vshiftins_v2i64(
|
||||
|
|
@ -952,6 +1040,7 @@ pub unsafe fn vsliq_n_u64<const N: i32>(a: uint64x2_t, b: uint64x2_t) -> uint64x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_p8<const N: i32>(a: poly8x8_t, b: poly8x8_t) -> poly8x8_t {
|
||||
static_assert_uimm_bits!(N, 3);
|
||||
let n = N as i8;
|
||||
|
|
@ -966,6 +1055,7 @@ pub unsafe fn vsli_n_p8<const N: i32>(a: poly8x8_t, b: poly8x8_t) -> poly8x8_t {
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_p8<const N: i32>(a: poly8x16_t, b: poly8x16_t) -> poly8x16_t {
|
||||
static_assert_uimm_bits!(N, 3);
|
||||
let n = N as i8;
|
||||
|
|
@ -980,6 +1070,7 @@ pub unsafe fn vsliq_n_p8<const N: i32>(a: poly8x16_t, b: poly8x16_t) -> poly8x16
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_p16<const N: i32>(a: poly16x4_t, b: poly16x4_t) -> poly16x4_t {
|
||||
static_assert_uimm_bits!(N, 4);
|
||||
let n = N as i16;
|
||||
|
|
@ -995,6 +1086,7 @@ pub unsafe fn vsli_n_p16<const N: i32>(a: poly16x4_t, b: poly16x4_t) -> poly16x4
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsli.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x8_t {
|
||||
static_assert_uimm_bits!(N, 4);
|
||||
let n = N as i16;
|
||||
|
|
@ -1012,6 +1104,7 @@ pub unsafe fn vsliq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x
|
|||
#[target_feature(enable = "neon,v7,aes")]
|
||||
#[cfg_attr(test, assert_instr("vsli.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsli_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1_t {
|
||||
static_assert!(0 <= N && N <= 63);
|
||||
transmute(vshiftins_v1i64(
|
||||
|
|
@ -1028,6 +1121,7 @@ pub unsafe fn vsli_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1
|
|||
#[target_feature(enable = "neon,v7,aes")]
|
||||
#[cfg_attr(test, assert_instr("vsli.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsliq_n_p64<const N: i32>(a: poly64x2_t, b: poly64x2_t) -> poly64x2_t {
|
||||
static_assert!(0 <= N && N <= 63);
|
||||
transmute(vshiftins_v2i64(
|
||||
|
|
@ -1041,6 +1135,7 @@ pub unsafe fn vsliq_n_p64<const N: i32>(a: poly64x2_t, b: poly64x2_t) -> poly64x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_s8<const N: i32>(a: int8x8_t, b: int8x8_t) -> int8x8_t {
|
||||
static_assert!(1 <= N && N <= 8);
|
||||
let n = -N as i8;
|
||||
|
|
@ -1051,6 +1146,7 @@ pub unsafe fn vsri_n_s8<const N: i32>(a: int8x8_t, b: int8x8_t) -> int8x8_t {
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_s8<const N: i32>(a: int8x16_t, b: int8x16_t) -> int8x16_t {
|
||||
static_assert!(1 <= N && N <= 8);
|
||||
let n = -N as i8;
|
||||
|
|
@ -1065,6 +1161,7 @@ pub unsafe fn vsriq_n_s8<const N: i32>(a: int8x16_t, b: int8x16_t) -> int8x16_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_s16<const N: i32>(a: int16x4_t, b: int16x4_t) -> int16x4_t {
|
||||
static_assert!(1 <= N && N <= 16);
|
||||
let n = -N as i16;
|
||||
|
|
@ -1075,6 +1172,7 @@ pub unsafe fn vsri_n_s16<const N: i32>(a: int16x4_t, b: int16x4_t) -> int16x4_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_s16<const N: i32>(a: int16x8_t, b: int16x8_t) -> int16x8_t {
|
||||
static_assert!(1 <= N && N <= 16);
|
||||
let n = -N as i16;
|
||||
|
|
@ -1085,6 +1183,7 @@ pub unsafe fn vsriq_n_s16<const N: i32>(a: int16x8_t, b: int16x8_t) -> int16x8_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_s32<const N: i32>(a: int32x2_t, b: int32x2_t) -> int32x2_t {
|
||||
static_assert!(1 <= N && N <= 32);
|
||||
vshiftins_v2i32(a, b, int32x2_t(-N, -N))
|
||||
|
|
@ -1094,6 +1193,7 @@ pub unsafe fn vsri_n_s32<const N: i32>(a: int32x2_t, b: int32x2_t) -> int32x2_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_s32<const N: i32>(a: int32x4_t, b: int32x4_t) -> int32x4_t {
|
||||
static_assert!(1 <= N && N <= 32);
|
||||
vshiftins_v4i32(a, b, int32x4_t(-N, -N, -N, -N))
|
||||
|
|
@ -1103,6 +1203,7 @@ pub unsafe fn vsriq_n_s32<const N: i32>(a: int32x4_t, b: int32x4_t) -> int32x4_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_s64<const N: i32>(a: int64x1_t, b: int64x1_t) -> int64x1_t {
|
||||
static_assert!(1 <= N && N <= 64);
|
||||
vshiftins_v1i64(a, b, int64x1_t(-N as i64))
|
||||
|
|
@ -1112,6 +1213,7 @@ pub unsafe fn vsri_n_s64<const N: i32>(a: int64x1_t, b: int64x1_t) -> int64x1_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_s64<const N: i32>(a: int64x2_t, b: int64x2_t) -> int64x2_t {
|
||||
static_assert!(1 <= N && N <= 64);
|
||||
vshiftins_v2i64(a, b, int64x2_t(-N as i64, -N as i64))
|
||||
|
|
@ -1121,6 +1223,7 @@ pub unsafe fn vsriq_n_s64<const N: i32>(a: int64x2_t, b: int64x2_t) -> int64x2_t
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_u8<const N: i32>(a: uint8x8_t, b: uint8x8_t) -> uint8x8_t {
|
||||
static_assert!(1 <= N && N <= 8);
|
||||
let n = -N as i8;
|
||||
|
|
@ -1135,6 +1238,7 @@ pub unsafe fn vsri_n_u8<const N: i32>(a: uint8x8_t, b: uint8x8_t) -> uint8x8_t {
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_u8<const N: i32>(a: uint8x16_t, b: uint8x16_t) -> uint8x16_t {
|
||||
static_assert!(1 <= N && N <= 8);
|
||||
let n = -N as i8;
|
||||
|
|
@ -1149,6 +1253,7 @@ pub unsafe fn vsriq_n_u8<const N: i32>(a: uint8x16_t, b: uint8x16_t) -> uint8x16
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_u16<const N: i32>(a: uint16x4_t, b: uint16x4_t) -> uint16x4_t {
|
||||
static_assert!(1 <= N && N <= 16);
|
||||
let n = -N as i16;
|
||||
|
|
@ -1163,6 +1268,7 @@ pub unsafe fn vsri_n_u16<const N: i32>(a: uint16x4_t, b: uint16x4_t) -> uint16x4
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_u16<const N: i32>(a: uint16x8_t, b: uint16x8_t) -> uint16x8_t {
|
||||
static_assert!(1 <= N && N <= 16);
|
||||
let n = -N as i16;
|
||||
|
|
@ -1177,6 +1283,7 @@ pub unsafe fn vsriq_n_u16<const N: i32>(a: uint16x8_t, b: uint16x8_t) -> uint16x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_u32<const N: i32>(a: uint32x2_t, b: uint32x2_t) -> uint32x2_t {
|
||||
static_assert!(1 <= N && N <= 32);
|
||||
transmute(vshiftins_v2i32(
|
||||
|
|
@ -1190,6 +1297,7 @@ pub unsafe fn vsri_n_u32<const N: i32>(a: uint32x2_t, b: uint32x2_t) -> uint32x2
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.32", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_u32<const N: i32>(a: uint32x4_t, b: uint32x4_t) -> uint32x4_t {
|
||||
static_assert!(1 <= N && N <= 32);
|
||||
transmute(vshiftins_v4i32(
|
||||
|
|
@ -1203,6 +1311,7 @@ pub unsafe fn vsriq_n_u32<const N: i32>(a: uint32x4_t, b: uint32x4_t) -> uint32x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_u64<const N: i32>(a: uint64x1_t, b: uint64x1_t) -> uint64x1_t {
|
||||
static_assert!(1 <= N && N <= 64);
|
||||
transmute(vshiftins_v1i64(
|
||||
|
|
@ -1216,6 +1325,7 @@ pub unsafe fn vsri_n_u64<const N: i32>(a: uint64x1_t, b: uint64x1_t) -> uint64x1
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_u64<const N: i32>(a: uint64x2_t, b: uint64x2_t) -> uint64x2_t {
|
||||
static_assert!(1 <= N && N <= 64);
|
||||
transmute(vshiftins_v2i64(
|
||||
|
|
@ -1229,6 +1339,7 @@ pub unsafe fn vsriq_n_u64<const N: i32>(a: uint64x2_t, b: uint64x2_t) -> uint64x
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_p8<const N: i32>(a: poly8x8_t, b: poly8x8_t) -> poly8x8_t {
|
||||
static_assert!(1 <= N && N <= 8);
|
||||
let n = -N as i8;
|
||||
|
|
@ -1243,6 +1354,7 @@ pub unsafe fn vsri_n_p8<const N: i32>(a: poly8x8_t, b: poly8x8_t) -> poly8x8_t {
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.8", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_p8<const N: i32>(a: poly8x16_t, b: poly8x16_t) -> poly8x16_t {
|
||||
static_assert!(1 <= N && N <= 8);
|
||||
let n = -N as i8;
|
||||
|
|
@ -1257,6 +1369,7 @@ pub unsafe fn vsriq_n_p8<const N: i32>(a: poly8x16_t, b: poly8x16_t) -> poly8x16
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_p16<const N: i32>(a: poly16x4_t, b: poly16x4_t) -> poly16x4_t {
|
||||
static_assert!(1 <= N && N <= 16);
|
||||
let n = -N as i16;
|
||||
|
|
@ -1271,6 +1384,7 @@ pub unsafe fn vsri_n_p16<const N: i32>(a: poly16x4_t, b: poly16x4_t) -> poly16x4
|
|||
#[target_feature(enable = "neon,v7")]
|
||||
#[cfg_attr(test, assert_instr("vsri.16", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x8_t {
|
||||
static_assert!(1 <= N && N <= 16);
|
||||
let n = -N as i16;
|
||||
|
|
@ -1288,6 +1402,7 @@ pub unsafe fn vsriq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x
|
|||
#[target_feature(enable = "neon,v7,aes")]
|
||||
#[cfg_attr(test, assert_instr("vsri.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsri_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1_t {
|
||||
static_assert!(1 <= N && N <= 64);
|
||||
transmute(vshiftins_v1i64(
|
||||
|
|
@ -1304,6 +1419,7 @@ pub unsafe fn vsri_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1
|
|||
#[target_feature(enable = "neon,v7,aes")]
|
||||
#[cfg_attr(test, assert_instr("vsri.64", N = 1))]
|
||||
#[rustc_legacy_const_generics(2)]
|
||||
#[unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")]
|
||||
pub unsafe fn vsriq_n_p64<const N: i32>(a: poly64x2_t, b: poly64x2_t) -> poly64x2_t {
|
||||
static_assert!(1 <= N && N <= 64);
|
||||
transmute(vshiftins_v2i64(
|
||||
|
|
|
|||
|
|
@ -79,6 +79,14 @@ pub use self::crypto::*;
|
|||
pub(crate) mod neon;
|
||||
#[cfg(target_endian = "little")]
|
||||
#[cfg(any(target_arch = "aarch64", target_feature = "v7", doc))]
|
||||
#[cfg_attr(
|
||||
not(target_arch = "arm"),
|
||||
stable(feature = "neon_intrinsics", since = "1.59.0")
|
||||
)]
|
||||
#[cfg_attr(
|
||||
target_arch = "arm",
|
||||
unstable(feature = "stdarch_arm_neon_intrinsics", issue = "111800")
|
||||
)]
|
||||
pub use self::neon::*;
|
||||
|
||||
#[cfg(test)]
|
||||
|
|
|
|||
File diff suppressed because it is too large
Load diff
File diff suppressed because it is too large
Load diff
|
|
@ -2517,13 +2517,18 @@ fn gen_arm(
|
|||
RDM => String::from("\n#[stable(feature = \"rdm_intrinsics\", since = \"1.62.0\")]"),
|
||||
_ => String::new(),
|
||||
};
|
||||
let stable_arm = match target {
|
||||
_ => String::from(
|
||||
"\n#[unstable(feature = \"stdarch_arm_neon_intrinsics\", issue = \"111800\")]",
|
||||
),
|
||||
};
|
||||
let function_doc = create_doc_string(current_comment, &name);
|
||||
format!(
|
||||
r#"
|
||||
{function_doc}
|
||||
#[inline]
|
||||
#[cfg(target_arch = "arm")]{target_feature_arm}
|
||||
#[cfg_attr(test, assert_instr({assert_arm}{const_assert}))]{const_legacy}
|
||||
#[cfg_attr(test, assert_instr({assert_arm}{const_assert}))]{const_legacy}{stable_arm}
|
||||
{call_arm}
|
||||
|
||||
{function_doc}
|
||||
|
|
@ -2575,12 +2580,17 @@ fn gen_arm(
|
|||
RDM => String::from("\n#[cfg_attr(not(target_arch = \"arm\"), stable(feature = \"rdm_intrinsics\", since = \"1.62.0\"))]"),
|
||||
_ => String::new(),
|
||||
};
|
||||
let stable_arm = match target {
|
||||
_ => {
|
||||
String::from("\n#[cfg_attr(target_arch = \"arm\", unstable(feature = \"stdarch_arm_neon_intrinsics\", issue = \"111800\"))]")
|
||||
}
|
||||
};
|
||||
format!(
|
||||
r#"
|
||||
{function_doc}
|
||||
#[inline]{target_feature}
|
||||
#[cfg_attr(all(test, target_arch = "arm"), assert_instr({assert_arm}{const_assert}))]
|
||||
#[cfg_attr(all(test, target_arch = "aarch64"), assert_instr({assert_aarch64}{const_assert}))]{const_legacy}{stable_aarch64}
|
||||
#[cfg_attr(all(test, target_arch = "aarch64"), assert_instr({assert_aarch64}{const_assert}))]{const_legacy}{stable_aarch64}{stable_arm}
|
||||
{call}
|
||||
"#,
|
||||
function_doc = create_doc_string(current_comment, &name),
|
||||
|
|
|
|||
Loading…
Add table
Add a link
Reference in a new issue