Skip to content

Commit 242f4a3

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 4abdda2 commit 242f4a3

4 files changed

Lines changed: 186 additions & 237 deletions

File tree

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

Lines changed: 36 additions & 36 deletions
Original file line numberDiff line numberDiff line change
@@ -11769,7 +11769,7 @@ pub unsafe fn vld1q_p16(ptr: *const p16) -> poly16x8_t {
1176911769
#[doc = "## Safety"]
1177011770
#[doc = " * Neon intrinsic unsafe"]
1177111771
#[inline]
11772-
#[target_feature(enable = "neon,aes")]
11772+
#[target_feature(enable = "neon")]
1177311773
#[cfg_attr(test, assert_instr(ldr))]
1177411774
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1177511775
pub unsafe fn vld1_p64(ptr: *const p64) -> poly64x1_t {
@@ -11780,7 +11780,7 @@ pub unsafe fn vld1_p64(ptr: *const p64) -> poly64x1_t {
1178011780
#[doc = "## Safety"]
1178111781
#[doc = " * Neon intrinsic unsafe"]
1178211782
#[inline]
11783-
#[target_feature(enable = "neon,aes")]
11783+
#[target_feature(enable = "neon")]
1178411784
#[cfg_attr(test, assert_instr(ldr))]
1178511785
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1178611786
pub unsafe fn vld1q_p64(ptr: *const p64) -> poly64x2_t {
@@ -11962,7 +11962,7 @@ pub unsafe fn vld2_lane_s64<const LANE: i32>(a: *const i64, b: int64x1x2_t) -> i
1196211962
#[doc = "## Safety"]
1196311963
#[doc = " * Neon intrinsic unsafe"]
1196411964
#[inline]
11965-
#[target_feature(enable = "neon,aes")]
11965+
#[target_feature(enable = "neon")]
1196611966
#[cfg_attr(test, assert_instr(ld2, LANE = 0))]
1196711967
#[rustc_legacy_const_generics(2)]
1196811968
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -11989,7 +11989,7 @@ pub unsafe fn vld2_lane_u64<const LANE: i32>(a: *const u64, b: uint64x1x2_t) ->
1198911989
#[doc = " * Neon intrinsic unsafe"]
1199011990
#[inline]
1199111991
#[cfg(target_endian = "little")]
11992-
#[target_feature(enable = "neon,aes")]
11992+
#[target_feature(enable = "neon")]
1199311993
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1199411994
#[cfg_attr(test, assert_instr(ld2r))]
1199511995
pub unsafe fn vld2q_dup_p64(a: *const p64) -> poly64x2x2_t {
@@ -12001,7 +12001,7 @@ pub unsafe fn vld2q_dup_p64(a: *const p64) -> poly64x2x2_t {
1200112001
#[doc = " * Neon intrinsic unsafe"]
1200212002
#[inline]
1200312003
#[cfg(target_endian = "big")]
12004-
#[target_feature(enable = "neon,aes")]
12004+
#[target_feature(enable = "neon")]
1200512005
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1200612006
#[cfg_attr(test, assert_instr(ld2r))]
1200712007
pub unsafe fn vld2q_dup_p64(a: *const p64) -> poly64x2x2_t {
@@ -12139,7 +12139,7 @@ pub unsafe fn vld2q_lane_s64<const LANE: i32>(a: *const i64, b: int64x2x2_t) ->
1213912139
#[doc = "## Safety"]
1214012140
#[doc = " * Neon intrinsic unsafe"]
1214112141
#[inline]
12142-
#[target_feature(enable = "neon,aes")]
12142+
#[target_feature(enable = "neon")]
1214312143
#[cfg_attr(test, assert_instr(ld2, LANE = 0))]
1214412144
#[rustc_legacy_const_generics(2)]
1214512145
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -12192,7 +12192,7 @@ pub unsafe fn vld2q_lane_p8<const LANE: i32>(a: *const p8, b: poly8x16x2_t) -> p
1219212192
#[doc = " * Neon intrinsic unsafe"]
1219312193
#[inline]
1219412194
#[cfg(target_endian = "little")]
12195-
#[target_feature(enable = "neon,aes")]
12195+
#[target_feature(enable = "neon")]
1219612196
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1219712197
#[cfg_attr(test, assert_instr(ld2))]
1219812198
pub unsafe fn vld2q_p64(a: *const p64) -> poly64x2x2_t {
@@ -12204,7 +12204,7 @@ pub unsafe fn vld2q_p64(a: *const p64) -> poly64x2x2_t {
1220412204
#[doc = " * Neon intrinsic unsafe"]
1220512205
#[inline]
1220612206
#[cfg(target_endian = "big")]
12207-
#[target_feature(enable = "neon,aes")]
12207+
#[target_feature(enable = "neon")]
1220812208
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1220912209
#[cfg_attr(test, assert_instr(ld2))]
1221012210
pub unsafe fn vld2q_p64(a: *const p64) -> poly64x2x2_t {
@@ -12320,7 +12320,7 @@ pub unsafe fn vld3_lane_f64<const LANE: i32>(a: *const f64, b: float64x1x3_t) ->
1232012320
#[doc = "## Safety"]
1232112321
#[doc = " * Neon intrinsic unsafe"]
1232212322
#[inline]
12323-
#[target_feature(enable = "neon,aes")]
12323+
#[target_feature(enable = "neon")]
1232412324
#[cfg_attr(test, assert_instr(ld3, LANE = 0))]
1232512325
#[rustc_legacy_const_generics(2)]
1232612326
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -12373,7 +12373,7 @@ pub unsafe fn vld3_lane_u64<const LANE: i32>(a: *const u64, b: uint64x1x3_t) ->
1237312373
#[doc = " * Neon intrinsic unsafe"]
1237412374
#[inline]
1237512375
#[cfg(target_endian = "little")]
12376-
#[target_feature(enable = "neon,aes")]
12376+
#[target_feature(enable = "neon")]
1237712377
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1237812378
#[cfg_attr(test, assert_instr(ld3r))]
1237912379
pub unsafe fn vld3q_dup_p64(a: *const p64) -> poly64x2x3_t {
@@ -12385,7 +12385,7 @@ pub unsafe fn vld3q_dup_p64(a: *const p64) -> poly64x2x3_t {
1238512385
#[doc = " * Neon intrinsic unsafe"]
1238612386
#[inline]
1238712387
#[cfg(target_endian = "big")]
12388-
#[target_feature(enable = "neon,aes")]
12388+
#[target_feature(enable = "neon")]
1238912389
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1239012390
#[cfg_attr(test, assert_instr(ld3r))]
1239112391
pub unsafe fn vld3q_dup_p64(a: *const p64) -> poly64x2x3_t {
@@ -12476,7 +12476,7 @@ pub unsafe fn vld3q_lane_f64<const LANE: i32>(a: *const f64, b: float64x2x3_t) -
1247612476
#[doc = "## Safety"]
1247712477
#[doc = " * Neon intrinsic unsafe"]
1247812478
#[inline]
12479-
#[target_feature(enable = "neon,aes")]
12479+
#[target_feature(enable = "neon")]
1248012480
#[cfg_attr(test, assert_instr(ld3, LANE = 0))]
1248112481
#[rustc_legacy_const_generics(2)]
1248212482
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -12581,7 +12581,7 @@ pub unsafe fn vld3q_lane_p8<const LANE: i32>(a: *const p8, b: poly8x16x3_t) -> p
1258112581
#[doc = " * Neon intrinsic unsafe"]
1258212582
#[inline]
1258312583
#[cfg(target_endian = "little")]
12584-
#[target_feature(enable = "neon,aes")]
12584+
#[target_feature(enable = "neon")]
1258512585
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1258612586
#[cfg_attr(test, assert_instr(ld3))]
1258712587
pub unsafe fn vld3q_p64(a: *const p64) -> poly64x2x3_t {
@@ -12593,7 +12593,7 @@ pub unsafe fn vld3q_p64(a: *const p64) -> poly64x2x3_t {
1259312593
#[doc = " * Neon intrinsic unsafe"]
1259412594
#[inline]
1259512595
#[cfg(target_endian = "big")]
12596-
#[target_feature(enable = "neon,aes")]
12596+
#[target_feature(enable = "neon")]
1259712597
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1259812598
#[cfg_attr(test, assert_instr(ld3))]
1259912599
pub unsafe fn vld3q_p64(a: *const p64) -> poly64x2x3_t {
@@ -12738,7 +12738,7 @@ pub unsafe fn vld4_lane_s64<const LANE: i32>(a: *const i64, b: int64x1x4_t) -> i
1273812738
#[doc = "## Safety"]
1273912739
#[doc = " * Neon intrinsic unsafe"]
1274012740
#[inline]
12741-
#[target_feature(enable = "neon,aes")]
12741+
#[target_feature(enable = "neon")]
1274212742
#[cfg_attr(test, assert_instr(ld4, LANE = 0))]
1274312743
#[rustc_legacy_const_generics(2)]
1274412744
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -12765,7 +12765,7 @@ pub unsafe fn vld4_lane_u64<const LANE: i32>(a: *const u64, b: uint64x1x4_t) ->
1276512765
#[doc = " * Neon intrinsic unsafe"]
1276612766
#[inline]
1276712767
#[cfg(target_endian = "little")]
12768-
#[target_feature(enable = "neon,aes")]
12768+
#[target_feature(enable = "neon")]
1276912769
#[cfg_attr(test, assert_instr(ld4r))]
1277012770
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1277112771
pub unsafe fn vld4q_dup_p64(a: *const p64) -> poly64x2x4_t {
@@ -12777,7 +12777,7 @@ pub unsafe fn vld4q_dup_p64(a: *const p64) -> poly64x2x4_t {
1277712777
#[doc = " * Neon intrinsic unsafe"]
1277812778
#[inline]
1277912779
#[cfg(target_endian = "big")]
12780-
#[target_feature(enable = "neon,aes")]
12780+
#[target_feature(enable = "neon")]
1278112781
#[cfg_attr(test, assert_instr(ld4r))]
1278212782
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1278312783
pub unsafe fn vld4q_dup_p64(a: *const p64) -> poly64x2x4_t {
@@ -12925,7 +12925,7 @@ pub unsafe fn vld4q_lane_s64<const LANE: i32>(a: *const i64, b: int64x2x4_t) ->
1292512925
#[doc = "## Safety"]
1292612926
#[doc = " * Neon intrinsic unsafe"]
1292712927
#[inline]
12928-
#[target_feature(enable = "neon,aes")]
12928+
#[target_feature(enable = "neon")]
1292912929
#[cfg_attr(test, assert_instr(ld4, LANE = 0))]
1293012930
#[rustc_legacy_const_generics(2)]
1293112931
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -12978,8 +12978,8 @@ pub unsafe fn vld4q_lane_p8<const LANE: i32>(a: *const p8, b: poly8x16x4_t) -> p
1297812978
#[doc = " * Neon intrinsic unsafe"]
1297912979
#[inline]
1298012980
#[cfg(target_endian = "little")]
12981+
#[target_feature(enable = "neon")]
1298112982
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
12982-
#[target_feature(enable = "neon,aes")]
1298312983
#[cfg_attr(test, assert_instr(ld4))]
1298412984
pub unsafe fn vld4q_p64(a: *const p64) -> poly64x2x4_t {
1298512985
transmute(vld4q_s64(transmute(a)))
@@ -12990,8 +12990,8 @@ pub unsafe fn vld4q_p64(a: *const p64) -> poly64x2x4_t {
1299012990
#[doc = " * Neon intrinsic unsafe"]
1299112991
#[inline]
1299212992
#[cfg(target_endian = "big")]
12993+
#[target_feature(enable = "neon")]
1299312994
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
12994-
#[target_feature(enable = "neon,aes")]
1299512995
#[cfg_attr(test, assert_instr(ld4))]
1299612996
pub unsafe fn vld4q_p64(a: *const p64) -> poly64x2x4_t {
1299712997
let mut ret_val: poly64x2x4_t = transmute(vld4q_s64(transmute(a)));
@@ -15397,7 +15397,7 @@ pub fn vmull_high_p64(a: poly64x2_t, b: poly64x2_t) -> p128 {
1539715397
#[doc = "Polynomial multiply long"]
1539815398
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vmull_high_p8)"]
1539915399
#[inline]
15400-
#[target_feature(enable = "neon")]
15400+
#[target_feature(enable = "neon,aes")]
1540115401
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
1540215402
#[cfg_attr(all(test, target_endian = "little"), assert_instr(pmull2))]
1540315403
pub fn vmull_high_p8(a: poly8x16_t, b: poly8x16_t) -> poly16x8_t {
@@ -23829,7 +23829,7 @@ pub fn vsliq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x8_t {
2382923829
#[doc = "Shift Left and Insert (immediate)"]
2383023830
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsli_n_p64)"]
2383123831
#[inline]
23832-
#[target_feature(enable = "neon,aes")]
23832+
#[target_feature(enable = "neon")]
2383323833
#[cfg_attr(test, assert_instr(sli, N = 1))]
2383423834
#[rustc_legacy_const_generics(2)]
2383523835
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -23840,7 +23840,7 @@ pub fn vsli_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1_t {
2384023840
#[doc = "Shift Left and Insert (immediate)"]
2384123841
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsliq_n_p64)"]
2384223842
#[inline]
23843-
#[target_feature(enable = "neon,aes")]
23843+
#[target_feature(enable = "neon")]
2384423844
#[cfg_attr(test, assert_instr(sli, N = 1))]
2384523845
#[rustc_legacy_const_generics(2)]
2384623846
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24489,7 +24489,7 @@ pub fn vsriq_n_p16<const N: i32>(a: poly16x8_t, b: poly16x8_t) -> poly16x8_t {
2448924489
#[doc = "Shift Right and Insert (immediate)"]
2449024490
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsri_n_p64)"]
2449124491
#[inline]
24492-
#[target_feature(enable = "neon,aes")]
24492+
#[target_feature(enable = "neon")]
2449324493
#[cfg_attr(test, assert_instr(sri, N = 1))]
2449424494
#[rustc_legacy_const_generics(2)]
2449524495
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24500,7 +24500,7 @@ pub fn vsri_n_p64<const N: i32>(a: poly64x1_t, b: poly64x1_t) -> poly64x1_t {
2450024500
#[doc = "Shift Right and Insert (immediate)"]
2450124501
#[doc = "[Arm's documentation](https://developer.arm.com/architectures/instruction-sets/intrinsics/vsriq_n_p64)"]
2450224502
#[inline]
24503-
#[target_feature(enable = "neon,aes")]
24503+
#[target_feature(enable = "neon")]
2450424504
#[cfg_attr(test, assert_instr(sri, N = 1))]
2450524505
#[rustc_legacy_const_generics(2)]
2450624506
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24849,7 +24849,7 @@ pub unsafe fn vst1q_p16(ptr: *mut p16, a: poly16x8_t) {
2484924849
#[doc = "## Safety"]
2485024850
#[doc = " * Neon intrinsic unsafe"]
2485124851
#[inline]
24852-
#[target_feature(enable = "neon,aes")]
24852+
#[target_feature(enable = "neon")]
2485324853
#[cfg_attr(test, assert_instr(str))]
2485424854
#[allow(clippy::cast_ptr_alignment)]
2485524855
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -24861,7 +24861,7 @@ pub unsafe fn vst1_p64(ptr: *mut p64, a: poly64x1_t) {
2486124861
#[doc = "## Safety"]
2486224862
#[doc = " * Neon intrinsic unsafe"]
2486324863
#[inline]
24864-
#[target_feature(enable = "neon,aes")]
24864+
#[target_feature(enable = "neon")]
2486524865
#[cfg_attr(test, assert_instr(str))]
2486624866
#[allow(clippy::cast_ptr_alignment)]
2486724867
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -25070,7 +25070,7 @@ pub unsafe fn vst2_lane_s64<const LANE: i32>(a: *mut i64, b: int64x1x2_t) {
2507025070
#[doc = "## Safety"]
2507125071
#[doc = " * Neon intrinsic unsafe"]
2507225072
#[inline]
25073-
#[target_feature(enable = "neon,aes")]
25073+
#[target_feature(enable = "neon")]
2507425074
#[cfg_attr(test, assert_instr(st2, LANE = 0))]
2507525075
#[rustc_legacy_const_generics(2)]
2507625076
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -25178,7 +25178,7 @@ pub unsafe fn vst2q_lane_s64<const LANE: i32>(a: *mut i64, b: int64x2x2_t) {
2517825178
#[doc = "## Safety"]
2517925179
#[doc = " * Neon intrinsic unsafe"]
2518025180
#[inline]
25181-
#[target_feature(enable = "neon,aes")]
25181+
#[target_feature(enable = "neon")]
2518225182
#[cfg_attr(test, assert_instr(st2, LANE = 0))]
2518325183
#[rustc_legacy_const_generics(2)]
2518425184
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
@@ -25230,7 +25230,7 @@ pub unsafe fn vst2q_lane_p8<const LANE: i32>(a: *mut p8, b: poly8x16x2_t) {
2523025230
#[doc = "## Safety"]
2523125231
#[doc = " * Neon intrinsic unsafe"]
2523225232
#[inline]
25233-
#[target_feature(enable = "neon,aes")]
25233+
#[target_feature(enable = "neon")]
2523425234
#[cfg_attr(test, assert_instr(st2))]
2523525235
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
2523625236
pub unsafe fn vst2q_p64(a: *mut p64, b: poly64x2x2_t) {
@@ -25303,8 +25303,8 @@ pub unsafe fn vst3_lane_s64<const LANE: i32>(a: *mut i64, b: int64x1x3_t) {
2530325303
#[doc = "## Safety"]
2530425304
#[doc = " * Neon intrinsic unsafe"]
2530525305
#[inline]
25306+
#[target_feature(enable = "neon")]
2530625307
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25307-
#[target_feature(enable = "neon,aes")]
2530825308
#[cfg_attr(test, assert_instr(st3, LANE = 0))]
2530925309
#[rustc_legacy_const_generics(2)]
2531025310
pub unsafe fn vst3_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x1x3_t) {
@@ -25411,8 +25411,8 @@ pub unsafe fn vst3q_lane_s64<const LANE: i32>(a: *mut i64, b: int64x2x3_t) {
2541125411
#[doc = "## Safety"]
2541225412
#[doc = " * Neon intrinsic unsafe"]
2541325413
#[inline]
25414+
#[target_feature(enable = "neon")]
2541425415
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25415-
#[target_feature(enable = "neon,aes")]
2541625416
#[cfg_attr(test, assert_instr(st3, LANE = 0))]
2541725417
#[rustc_legacy_const_generics(2)]
2541825418
pub unsafe fn vst3q_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x2x3_t) {
@@ -25463,8 +25463,8 @@ pub unsafe fn vst3q_lane_p8<const LANE: i32>(a: *mut p8, b: poly8x16x3_t) {
2546325463
#[doc = "## Safety"]
2546425464
#[doc = " * Neon intrinsic unsafe"]
2546525465
#[inline]
25466+
#[target_feature(enable = "neon")]
2546625467
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25467-
#[target_feature(enable = "neon,aes")]
2546825468
#[cfg_attr(test, assert_instr(st3))]
2546925469
pub unsafe fn vst3q_p64(a: *mut p64, b: poly64x2x3_t) {
2547025470
vst3q_s64(transmute(a), transmute(b))
@@ -25550,8 +25550,8 @@ pub unsafe fn vst4_lane_s64<const LANE: i32>(a: *mut i64, b: int64x1x4_t) {
2555025550
#[doc = "## Safety"]
2555125551
#[doc = " * Neon intrinsic unsafe"]
2555225552
#[inline]
25553+
#[target_feature(enable = "neon")]
2555325554
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25554-
#[target_feature(enable = "neon,aes")]
2555525555
#[cfg_attr(test, assert_instr(st4, LANE = 0))]
2555625556
#[rustc_legacy_const_generics(2)]
2555725557
pub unsafe fn vst4_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x1x4_t) {
@@ -25679,8 +25679,8 @@ pub unsafe fn vst4q_lane_s64<const LANE: i32>(a: *mut i64, b: int64x2x4_t) {
2567925679
#[doc = "## Safety"]
2568025680
#[doc = " * Neon intrinsic unsafe"]
2568125681
#[inline]
25682+
#[target_feature(enable = "neon")]
2568225683
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25683-
#[target_feature(enable = "neon,aes")]
2568425684
#[cfg_attr(test, assert_instr(st4, LANE = 0))]
2568525685
#[rustc_legacy_const_generics(2)]
2568625686
pub unsafe fn vst4q_lane_p64<const LANE: i32>(a: *mut p64, b: poly64x2x4_t) {
@@ -25731,8 +25731,8 @@ pub unsafe fn vst4q_lane_p8<const LANE: i32>(a: *mut p8, b: poly8x16x4_t) {
2573125731
#[doc = "## Safety"]
2573225732
#[doc = " * Neon intrinsic unsafe"]
2573325733
#[inline]
25734+
#[target_feature(enable = "neon")]
2573425735
#[stable(feature = "neon_intrinsics", since = "1.59.0")]
25735-
#[target_feature(enable = "neon,aes")]
2573625736
#[cfg_attr(test, assert_instr(st4))]
2573725737
pub unsafe fn vst4q_p64(a: *mut p64, b: poly64x2x4_t) {
2573825738
vst4q_s64(transmute(a), transmute(b))

0 commit comments

Comments
 (0)