Skip to content

Commit 4e13a78

Browse files
adamgemmelladamgemmell
committed
Remove the aes feature from many arm intrinsics
The exceptions to this are the vaes* intrinsics, and ones using the P64 variants of PMULL[2] instructions
1 parent d940579 commit 4e13a78

4 files changed

Lines changed: 85 additions & 136 deletions

File tree

‎crates/core_arch/src/aarch64/neon/generated.rs‎

Lines changed: 30 additions & 30 deletions
Original file line numberDiff line numberDiff line change
@@ -10212,7 +10212,7 @@ pub unsafe fn vld1q_p16(ptr: *const p16) -> poly16x8_t {
1021210212
#[doc = "## Safety"]
1021310213
#[doc = " * Neon intrinsic unsafe"]
1021410214
#[inline]
10215-
#[target_feature(enable = "neon,aes")]
10215+
#[target_feature(enable = "neon")]
1021610216
#[cfg_attr(test, assert_instr(ldr))]
1021710217
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1021810218
pub unsafe fn vld1_p64(ptr: *const p64) -> poly64x1_t {
@@ -10223,7 +10223,7 @@ pub unsafe fn vld1_p64(ptr: *const p64) -> poly64x1_t {
1022310223
#[doc = "## Safety"]
1022410224
#[doc = " * Neon intrinsic unsafe"]
1022510225
#[inline]
10226-
#[target_feature(enable = "neon,aes")]
10226+
#[target_feature(enable = "neon")]
1022710227
#[cfg_attr(test, assert_instr(ldr))]
1022810228
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1022910229
pub unsafe fn vld1q_p64(ptr: *const p64) -> poly64x2_t {
@@ -10405,7 +10405,7 @@ pub unsafe fn vld2_lane_s64<const LANE: i32>(a: *const i64, b: int64x1x2_t) -> i
1040510405
#[doc = "## Safety"]
1040610406
#[doc = " * Neon intrinsic unsafe"]
1040710407
#[inline]
10408-
#[target_feature(enable = "neon,aes")]
10408+
#[target_feature(enable = "neon")]
1040910409
#[cfg_attr(test, assert_instr(ld2, LANE = 0))]
1041010410
#[rustc_legacy_const_generics(2)]
1041110411
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -10431,7 +10431,7 @@ pub unsafe fn vld2_lane_u64<const LANE: i32>(a: *const u64, b: uint64x1x2_t) ->
1043110431
#[doc = "## Safety"]
1043210432
#[doc = " * Neon intrinsic unsafe"]
1043310433
#[inline]
10434-
#[target_feature(enable = "neon,aes")]
10434+
#[target_feature(enable = "neon")]
1043510435
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1043610436
#[cfg_attr(test, assert_instr(ld2r))]
1043710437
pub unsafe fn vld2q_dup_p64(a: *const p64) -> poly64x2x2_t {
@@ -10550,7 +10550,7 @@ pub unsafe fn vld2q_lane_s64<const LANE: i32>(a: *const i64, b: int64x2x2_t) ->
1055010550
#[doc = "## Safety"]
1055110551
#[doc = " * Neon intrinsic unsafe"]
1055210552
#[inline]
10553-
#[target_feature(enable = "neon,aes")]
10553+
#[target_feature(enable = "neon")]
1055410554
#[cfg_attr(test, assert_instr(ld2, LANE = 0))]
1055510555
#[rustc_legacy_const_generics(2)]
1055610556
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -10602,7 +10602,7 @@ pub unsafe fn vld2q_lane_p8<const LANE: i32>(a: *const p8, b: poly8x16x2_t) -> p
1060210602
#[doc = "## Safety"]
1060310603
#[doc = " * Neon intrinsic unsafe"]
1060410604
#[inline]
10605-
#[target_feature(enable = "neon,aes")]
10605+
#[target_feature(enable = "neon")]
1060610606
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1060710607
#[cfg_attr(test, assert_instr(ld2))]
1060810608
pub unsafe fn vld2q_p64(a: *const p64) -> poly64x2x2_t {
@@ -10715,7 +10715,7 @@ pub unsafe fn vld3_lane_f64<const LANE: i32>(a: *const f64, b: float64x1x3_t) ->
1071510715
#[doc = "## Safety"]
1071610716
#[doc = " * Neon intrinsic unsafe"]
1071710717
#[inline]
10718-
#[target_feature(enable = "neon,aes")]
10718+
#[target_feature(enable = "neon")]
1071910719
#[cfg_attr(test, assert_instr(ld3, LANE = 0))]
1072010720
#[rustc_legacy_const_generics(2)]
1072110721
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -10767,7 +10767,7 @@ pub unsafe fn vld3_lane_u64<const LANE: i32>(a: *const u64, b: uint64x1x3_t) ->
1076710767
#[doc = "## Safety"]
1076810768
#[doc = " * Neon intrinsic unsafe"]
1076910769
#[inline]
10770-
#[target_feature(enable = "neon,aes")]
10770+
#[target_feature(enable = "neon")]
1077110771
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1077210772
#[cfg_attr(test, assert_instr(ld3r))]
1077310773
pub unsafe fn vld3q_dup_p64(a: *const p64) -> poly64x2x3_t {
@@ -10837,7 +10837,7 @@ pub unsafe fn vld3q_lane_f64<const LANE: i32>(a: *const f64, b: float64x2x3_t) -
1083710837
#[doc = "## Safety"]
1083810838
#[doc = " * Neon intrinsic unsafe"]
1083910839
#[inline]
10840-
#[target_feature(enable = "neon,aes")]
10840+
#[target_feature(enable = "neon")]
1084110841
#[cfg_attr(test, assert_instr(ld3, LANE = 0))]
1084210842
#[rustc_legacy_const_generics(2)]
1084310843
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -10941,7 +10941,7 @@ pub unsafe fn vld3q_lane_p8<const LANE: i32>(a: *const p8, b: poly8x16x3_t) -> p
1094110941
#[doc = "## Safety"]
1094210942
#[doc = " * Neon intrinsic unsafe"]
1094310943
#[inline]
10944-
#[target_feature(enable = "neon,aes")]
10944+
#[target_feature(enable = "neon")]
1094510945
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1094610946
#[cfg_attr(test, assert_instr(ld3))]
1094710947
pub unsafe fn vld3q_p64(a: *const p64) -> poly64x2x3_t {
@@ -11082,7 +11082,7 @@ pub unsafe fn vld4_lane_s64<const LANE: i32>(a: *const i64, b: int64x1x4_t) -> i
1108211082
#[doc = "## Safety"]
1108311083
#[doc = " * Neon intrinsic unsafe"]
1108411084
#[inline]
11085-
#[target_feature(enable = "neon,aes")]
11085+
#[target_feature(enable = "neon")]
1108611086
#[cfg_attr(test, assert_instr(ld4, LANE = 0))]
1108711087
#[rustc_legacy_const_generics(2)]
1108811088
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -11108,7 +11108,7 @@ pub unsafe fn vld4_lane_u64<const LANE: i32>(a: *const u64, b: uint64x1x4_t) ->
1110811108
#[doc = "## Safety"]
1110911109
#[doc = " * Neon intrinsic unsafe"]
1111011110
#[inline]
11111-
#[target_feature(enable = "neon,aes")]
11111+
#[target_feature(enable = "neon")]
1111211112
#[cfg_attr(test, assert_instr(ld4r))]
1111311113
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1111411114
pub unsafe fn vld4q_dup_p64(a: *const p64) -> poly64x2x4_t {
@@ -11233,7 +11233,7 @@ pub unsafe fn vld4q_lane_s64<const LANE: i32>(a: *const i64, b: int64x2x4_t) ->
1123311233
#[doc = "## Safety"]
1123411234
#[doc = " * Neon intrinsic unsafe"]
1123511235
#[inline]
11236-
#[target_feature(enable = "neon,aes")]
11236+
#[target_feature(enable = "neon")]
1123711237
#[cfg_attr(test, assert_instr(ld4, LANE = 0))]
1123811238
#[rustc_legacy_const_generics(2)]
1123911239
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -11285,8 +11285,8 @@ pub unsafe fn vld4q_lane_p8<const LANE: i32>(a: *const p8, b: poly8x16x4_t) -> p
1128511285
#[doc = "## Safety"]
1128611286
#[doc = " * Neon intrinsic unsafe"]
1128711287
#[inline]
11288+
#[target_feature(enable = "neon")]
1128811289
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
11289-
#[target_feature(enable = "neon,aes")]
1129011290
#[cfg_attr(test, assert_instr(ld4))]
1129111291
pub unsafe fn vld4q_p64(a: *const p64) -> poly64x2x4_t {
1129211292
transmute(vld4q_s64(transmute(a)))
@@ -13627,7 +13627,7 @@ pub fn vmull_high_p64(a: poly64x2_t, b: poly64x2_t) -> p128 {
1362713627
#[doc = "Polynomial multiply long"]
1362813628
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vmull_high_p8)"]
1362913629
#[inline]
13630-
#[target_feature(enable = "neon")]
13630+
#[target_feature(enable = "neon,aes")]
1363113631
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1363213632
#[cfg_attr(all(test, target_endian = "little"), assert_instr(pmull2))]
1363313633
pub fn vmull_high_p8(a: poly8x16_t, b: poly8x16_t) -> poly16x8_t {
@@ -23689,7 +23689,7 @@ pub fn vsliq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x8_t {
2368923689
#[doc = "Shift Left and Insert (immediate)"]
2369023690
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsli_n_p64)"]
2369123691
#[inline]
23692-
#[target_feature(enable = "neon,aes")]
23692+
#[target_feature(enable = "neon")]
2369323693
#[cfg_attr(test, assert_instr(sli, N = 1))]
2369423694
#[rustc_legacy_const_generics(2)]
2369523695
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -23700,7 +23700,7 @@ pub fn vsli_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1_t {
2370023700
#[doc = "Shift Left and Insert (immediate)"]
2370123701
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsliq_n_p64)"]
2370223702
#[inline]
23703-
#[target_feature(enable = "neon,aes")]
23703+
#[target_feature(enable = "neon")]
2370423704
#[cfg_attr(test, assert_instr(sli, N = 1))]
2370523705
#[rustc_legacy_const_generics(2)]
2370623706
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24571,7 +24571,7 @@ pub fn vsriq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x8_t {
2457124571
#[doc = "Shift Right and Insert (immediate)"]
2457224572
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsri_n_p64)"]
2457324573
#[inline]
24574-
#[target_feature(enable = "neon,aes")]
24574+
#[target_feature(enable = "neon")]
2457524575
#[cfg_attr(test, assert_instr(sri, N = 1))]
2457624576
#[rustc_legacy_const_generics(2)]
2457724577
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24582,7 +24582,7 @@ pub fn vsri_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1_t {
2458224582
#[doc = "Shift Right and Insert (immediate)"]
2458324583
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsriq_n_p64)"]
2458424584
#[inline]
24585-
#[target_feature(enable = "neon,aes")]
24585+
#[target_feature(enable = "neon")]
2458624586
#[cfg_attr(test, assert_instr(sri, N = 1))]
2458724587
#[rustc_legacy_const_generics(2)]
2458824588
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24931,7 +24931,7 @@ pub unsafe fn vst1q_p16(ptr: *mut p16, a: poly16x8_t) {
2493124931
#[doc = "## Safety"]
2493224932
#[doc = " * Neon intrinsic unsafe"]
2493324933
#[inline]
24934-
#[target_feature(enable = "neon,aes")]
24934+
#[target_feature(enable = "neon")]
2493524935
#[cfg_attr(test, assert_instr(str))]
2493624936
#[allow(clippy::cast_ptr_alignment)]
2493724937
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24943,7 +24943,7 @@ pub unsafe fn vst1_p64(ptr: *mut p64, a: poly64x1_t) {
2494324943
#[doc = "## Safety"]
2494424944
#[doc = " * Neon intrinsic unsafe"]
2494524945
#[inline]
24946-
#[target_feature(enable = "neon,aes")]
24946+
#[target_feature(enable = "neon")]
2494724947
#[cfg_attr(test, assert_instr(str))]
2494824948
#[allow(clippy::cast_ptr_alignment)]
2494924949
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -25152,7 +25152,7 @@ pub unsafe fn vst2_lane_s64<const LANE: i32>(a: *mut i64, b: int64x1x2_t) {
2515225152
#[doc = "## Safety"]
2515325153
#[doc = " * Neon intrinsic unsafe"]
2515425154
#[inline]
25155-
#[target_feature(enable = "neon,aes")]
25155+
#[target_feature(enable = "neon")]
2515625156
#[cfg_attr(test, assert_instr(st2, LANE = 0))]
2515725157
#[rustc_legacy_const_generics(2)]
2515825158
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -25260,7 +25260,7 @@ pub unsafe fn vst2q_lane_s64<const LANE: i32>(a: *mut i64, b: int64x2x2_t) {
2526025260
#[doc = "## Safety"]
2526125261
#[doc = " * Neon intrinsic unsafe"]
2526225262
#[inline]
25263-
#[target_feature(enable = "neon,aes")]
25263+
#[target_feature(enable = "neon")]
2526425264
#[cfg_attr(test, assert_instr(st2, LANE = 0))]
2526525265
#[rustc_legacy_const_generics(2)]
2526625266
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -25312,7 +25312,7 @@ pub unsafe fn vst2q_lane_p8<const LANE: i32>(a: *mut p8, b: poly8x16x2_t) {
2531225312
#[doc = "## Safety"]
2531325313
#[doc = " * Neon intrinsic unsafe"]
2531425314
#[inline]
25315-
#[target_feature(enable = "neon,aes")]
25315+
#[target_feature(enable = "neon")]
2531625316
#[cfg_attr(test, assert_instr(st2))]
2531725317
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
2531825318
pub unsafe fn vst2q_p64(a: *mut p64, b: poly64x2x2_t) {
@@ -25385,8 +25385,8 @@ pub unsafe fn vst3_lane_s64<const LANE: i32>(a: *mut i64, b: int64x1x3_t) {
2538525385
#[doc = "## Safety"]
2538625386
#[doc = " * Neon intrinsic unsafe"]
2538725387
#[inline]
25388+
#[target_feature(enable = "neon")]
2538825389
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25389-
#[target_feature(enable = "neon,aes")]
2539025390
#[cfg_attr(test, assert_instr(st3, LANE = 0))]
2539125391
#[rustc_legacy_const_generics(2)]
2539225392
pub unsafe fn vst3_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x1x3_t) {
@@ -25493,8 +25493,8 @@ pub unsafe fn vst3q_lane_s64<const LANE: i32>(a: *mut i64, b: int64x2x3_t) {
2549325493
#[doc = "## Safety"]
2549425494
#[doc = " * Neon intrinsic unsafe"]
2549525495
#[inline]
25496+
#[target_feature(enable = "neon")]
2549625497
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25497-
#[target_feature(enable = "neon,aes")]
2549825498
#[cfg_attr(test, assert_instr(st3, LANE = 0))]
2549925499
#[rustc_legacy_const_generics(2)]
2550025500
pub unsafe fn vst3q_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x2x3_t) {
@@ -25545,8 +25545,8 @@ pub unsafe fn vst3q_lane_p8<const LANE: i32>(a: *mut p8, b: poly8x16x3_t) {
2554525545
#[doc = "## Safety"]
2554625546
#[doc = " * Neon intrinsic unsafe"]
2554725547
#[inline]
25548+
#[target_feature(enable = "neon")]
2554825549
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25549-
#[target_feature(enable = "neon,aes")]
2555025550
#[cfg_attr(test, assert_instr(st3))]
2555125551
pub unsafe fn vst3q_p64(a: *mut p64, b: poly64x2x3_t) {
2555225552
vst3q_s64(transmute(a), transmute(b))
@@ -25632,8 +25632,8 @@ pub unsafe fn vst4_lane_s64<const LANE: i32>(a: *mut i64, b: int64x1x4_t) {
2563225632
#[doc = "## Safety"]
2563325633
#[doc = " * Neon intrinsic unsafe"]
2563425634
#[inline]
25635+
#[target_feature(enable = "neon")]
2563525636
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25636-
#[target_feature(enable = "neon,aes")]
2563725637
#[cfg_attr(test, assert_instr(st4, LANE = 0))]
2563825638
#[rustc_legacy_const_generics(2)]
2563925639
pub unsafe fn vst4_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x1x4_t) {
@@ -25761,8 +25761,8 @@ pub unsafe fn vst4q_lane_s64<const LANE: i32>(a: *mut i64, b: int64x2x4_t) {
2576125761
#[doc = "## Safety"]
2576225762
#[doc = " * Neon intrinsic unsafe"]
2576325763
#[inline]
25764+
#[target_feature(enable = "neon")]
2576425765
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25765-
#[target_feature(enable = "neon,aes")]
2576625766
#[cfg_attr(test, assert_instr(st4, LANE = 0))]
2576725767
#[rustc_legacy_const_generics(2)]
2576825768
pub unsafe fn vst4q_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x2x4_t) {
@@ -25813,8 +25813,8 @@ pub unsafe fn vst4q_lane_p8<const LANE: i32>(a: *mut p8, b: poly8x16x4_t) {
2581325813
#[doc = "## Safety"]
2581425814
#[doc = " * Neon intrinsic unsafe"]
2581525815
#[inline]
25816+
#[target_feature(enable = "neon")]
2581625817
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25817-
#[target_feature(enable = "neon,aes")]
2581825818
#[cfg_attr(test, assert_instr(st4))]
2581925819
pub unsafe fn vst4q_p64(a: *mut p64, b: poly64x2x4_t) {
2582025820
vst4q_s64(transmute(a), transmute(b))

0 commit comments

Comments
 (0)