| /arch/loongarch/lib/ |
| A D | xor_template.c | 18 const unsigned long * __restrict v2) 25 LD_AND_XOR_LINE(v2) 27 : : [v1] "r"(v1), [v2] "r"(v2) : "memory" 31 v2 += LINE_WIDTH / sizeof(unsigned long); 37 const unsigned long * __restrict v2, 45 LD_AND_XOR_LINE(v2) 48 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory" 68 LD_AND_XOR_LINE(v2) 72 : : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3), [v4] "r"(v4) 95 LD_AND_XOR_LINE(v2) [all …]
|
| /arch/s390/include/asm/ |
| A D | fpu-insn.h | 143 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3) in fpu_vab() 151 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3) in fpu_vcksm() 159 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3) in fpu_vesravb() 167 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3), [v4] "I" (v4) in fpu_vgfmag() 175 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3) in fpu_vgfmg() 314 : [v1] "I" (v1), [v2] "I" (v2) in fpu_vlr() 330 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3) in fpu_vn() 338 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3), [v4] "I" (v4) in fpu_vperm() 354 : [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3) in fpu_vsrlb() 458 : [v1] "I" (v1), [v2] "I" (v2) in fpu_vupllf() [all …]
|
| A D | fpu-insn-asm.h | 100 .ifc \vxr,%v2 224 .if \v2 & 0x10 308 .macro VLR v1, v2 310 VX_NUM v2, \v2 445 VX_NUM v2, \vr2 456 VX_NUM v2, \vr2 474 VX_NUM v2, \vr2 505 VX_NUM v2, \vr2 527 VX_NUM v2, \vr2 571 VX_NUM v2, \vr2 [all …]
|
| /arch/powerpc/lib/ |
| A D | xor_vmx.c | 57 DEFINE(v2); in __xor_altivec_2() 62 LOAD(v2); in __xor_altivec_2() 67 v2 += 4; in __xor_altivec_2() 77 DEFINE(v2); in __xor_altivec_3() 83 LOAD(v2); in __xor_altivec_3() 90 v2 += 4; in __xor_altivec_3() 102 DEFINE(v2); in __xor_altivec_4() 109 LOAD(v2); in __xor_altivec_4() 118 v2 += 4; in __xor_altivec_4() 140 LOAD(v2); in __xor_altivec_5() [all …]
|
| /arch/arm64/lib/ |
| A D | xor-neon.c | 32 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_2() 61 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_3() 67 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_3() 99 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_4() 105 v2 = veorq_u64(v2, vld1q_u64(dp4 + 4)); in xor_arm64_neon_4() 111 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_4() 146 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_5() 152 v2 = veorq_u64(v2, vld1q_u64(dp4 + 4)); in xor_arm64_neon_5() 158 v2 = veorq_u64(v2, vld1q_u64(dp5 + 4)); in xor_arm64_neon_5() 257 v2 = veorq_u64(v2, vld1q_u64(dp4 + 4)); in xor_arm64_eor3_4() [all …]
|
| /arch/arm64/boot/dts/rockchip/ |
| A D | rk3588j.dtsi | 11 compatible = "operating-points-v2"; 28 compatible = "operating-points-v2"; 49 compatible = "operating-points-v2"; 70 compatible = "operating-points-v2"; 96 operating-points-v2 = <&cluster1_opp_table>; 100 operating-points-v2 = <&cluster1_opp_table>; 104 operating-points-v2 = <&cluster2_opp_table>; 108 operating-points-v2 = <&cluster2_opp_table>; 112 operating-points-v2 = <&cluster0_opp_table>; 116 operating-points-v2 = <&cluster0_opp_table>; [all …]
|
| A D | rk3399-t.dtsi | 11 compatible = "operating-points-v2"; 34 compatible = "operating-points-v2"; 69 compatible = "operating-points-v2"; 91 operating-points-v2 = <&cluster0_opp>; 95 operating-points-v2 = <&cluster0_opp>; 99 operating-points-v2 = <&cluster0_opp>; 103 operating-points-v2 = <&cluster0_opp>; 107 operating-points-v2 = <&cluster1_opp>; 111 operating-points-v2 = <&cluster1_opp>; 115 operating-points-v2 = <&gpu_opp_table>;
|
| A D | rk3588-opp.dtsi | 5 compatible = "operating-points-v2"; 37 compatible = "operating-points-v2"; 78 compatible = "operating-points-v2"; 119 compatible = "operating-points-v2"; 157 operating-points-v2 = <&cluster1_opp_table>; 161 operating-points-v2 = <&cluster1_opp_table>; 165 operating-points-v2 = <&cluster2_opp_table>; 169 operating-points-v2 = <&cluster2_opp_table>; 173 operating-points-v2 = <&cluster0_opp_table>; 177 operating-points-v2 = <&cluster0_opp_table>; [all …]
|
| A D | rk3399-op1.dtsi | 10 compatible = "operating-points-v2"; 45 compatible = "operating-points-v2"; 88 compatible = "operating-points-v2"; 117 compatible = "operating-points-v2"; 139 operating-points-v2 = <&cluster0_opp>; 143 operating-points-v2 = <&cluster0_opp>; 147 operating-points-v2 = <&cluster0_opp>; 151 operating-points-v2 = <&cluster0_opp>; 155 operating-points-v2 = <&cluster1_opp>; 159 operating-points-v2 = <&cluster1_opp>; [all …]
|
| A D | rk3399-s.dtsi | 10 compatible = "operating-points-v2"; 33 compatible = "operating-points-v2"; 68 compatible = "operating-points-v2"; 98 operating-points-v2 = <&cluster0_opp>; 102 operating-points-v2 = <&cluster0_opp>; 106 operating-points-v2 = <&cluster0_opp>; 110 operating-points-v2 = <&cluster0_opp>; 114 operating-points-v2 = <&cluster1_opp>; 118 operating-points-v2 = <&cluster1_opp>; 122 operating-points-v2 = <&gpu_opp_table>;
|
| A D | rk3399.dtsi | 10 compatible = "operating-points-v2"; 41 compatible = "operating-points-v2"; 80 compatible = "operating-points-v2"; 110 operating-points-v2 = <&cluster0_opp>; 114 operating-points-v2 = <&cluster0_opp>; 118 operating-points-v2 = <&cluster0_opp>; 122 operating-points-v2 = <&cluster0_opp>; 126 operating-points-v2 = <&cluster1_opp>; 130 operating-points-v2 = <&cluster1_opp>; 134 operating-points-v2 = <&gpu_opp_table>;
|
| A D | rk3566t.dtsi | 7 compatible = "operating-points-v2"; 43 compatible = "operating-points-v2"; 73 operating-points-v2 = <&cpu0_opp_table>; 77 operating-points-v2 = <&cpu0_opp_table>; 81 operating-points-v2 = <&cpu0_opp_table>; 85 operating-points-v2 = <&cpu0_opp_table>; 89 operating-points-v2 = <&gpu_opp_table>;
|
| A D | rk3566.dtsi | 7 compatible = "operating-points-v2"; 55 compatible = "operating-points-v2"; 90 operating-points-v2 = <&cpu0_opp_table>; 94 operating-points-v2 = <&cpu0_opp_table>; 98 operating-points-v2 = <&cpu0_opp_table>; 102 operating-points-v2 = <&cpu0_opp_table>; 106 operating-points-v2 = <&gpu_opp_table>;
|
| /arch/mips/kernel/ |
| A D | r4k-bugs64.c | 44 void mult_sh_align_mod(long *v1, long *v2, long *w, in mult_sh_align_mod() argument 115 *v2 = lv2; in mult_sh_align_mod() 121 long v1[8], v2[8], w[8]; in check_mult_sh() local 135 mult_sh_align_mod(&v1[0], &v2[0], &w[0], 32, 0); in check_mult_sh() 136 mult_sh_align_mod(&v1[1], &v2[1], &w[1], 32, 1); in check_mult_sh() 137 mult_sh_align_mod(&v1[2], &v2[2], &w[2], 32, 2); in check_mult_sh() 138 mult_sh_align_mod(&v1[3], &v2[3], &w[3], 32, 3); in check_mult_sh() 139 mult_sh_align_mod(&v1[4], &v2[4], &w[4], 32, 4); in check_mult_sh() 140 mult_sh_align_mod(&v1[5], &v2[5], &w[5], 32, 5); in check_mult_sh() 141 mult_sh_align_mod(&v1[6], &v2[6], &w[6], 32, 6); in check_mult_sh() [all …]
|
| /arch/arm64/boot/dts/exynos/ |
| A D | exynos5433-bus.dtsi | 14 operating-points-v2 = <&bus_g2d_400_opp_table>; 22 operating-points-v2 = <&bus_g2d_266_opp_table>; 30 operating-points-v2 = <&bus_gscl_opp_table>; 38 operating-points-v2 = <&bus_hevc_opp_table>; 70 operating-points-v2 = <&bus_hevc_opp_table>; 78 operating-points-v2 = <&bus_hevc_opp_table>; 91 compatible = "operating-points-v2"; 121 compatible = "operating-points-v2"; 141 compatible = "operating-points-v2"; 155 compatible = "operating-points-v2"; [all …]
|
| /arch/arm64/crypto/ |
| A D | aes-ce-ccm-core.S | 65 ld1 {v2.16b}, [x1], #16 /* load next input block */ 67 eor v2.16b, v2.16b, v5.16b /* final round enc+mac */ 68 eor v6.16b, v1.16b, v2.16b /* xor with crypted ctr */ 70 eor v2.16b, v2.16b, v1.16b /* xor with crypted ctr */ 71 eor v6.16b, v2.16b, v5.16b /* final round enc */ 73 eor v0.16b, v0.16b, v2.16b /* xor mac with pt ^ rk[last] */ 96 ld1 {v2.16b}, [x1] /* load a full block of input */ 98 eor v7.16b, v2.16b, v1.16b /* encrypt partial input block */ 99 bif v2.16b, v7.16b, v22.16b /* select plaintext */ 101 tbl v2.16b, {v2.16b}, v9.16b /* copy plaintext to start of v2 */ [all …]
|
| A D | sm3-ce-core.S | 97 CPU_LE( rev32 v2.16b, v2.16b ) 102 qround a, v0, v1, v2, v3, v4 103 qround a, v1, v2, v3, v4, v0 104 qround a, v2, v3, v4, v0, v1 105 qround a, v3, v4, v0, v1, v2 109 qround b, v4, v0, v1, v2, v3 110 qround b, v0, v1, v2, v3, v4 111 qround b, v1, v2, v3, v4, v0 112 qround b, v2, v3, v4, v0, v1 113 qround b, v3, v4, v0, v1, v2 [all …]
|
| A D | aes-ce-core.S | 20 0: mov v2.16b, v1.16b 22 1: aese v0.16b, v2.16b 27 3: ld1 {v2.4s}, [x0], #16 33 aese v0.16b, v2.16b 48 0: mov v2.16b, v1.16b 50 1: aesd v0.16b, v2.16b 55 3: ld1 {v2.4s}, [x0], #16 61 aesd v0.16b, v2.16b
|
| A D | sm4-ce-core.S | 183 eor v2.16b, v2.16b, v1.16b 390 eor v2.16b, v2.16b, v1.16b 448 eor v2.16b, v2.16b, v10.16b 480 eor v2.16b, v2.16b, v10.16b 569 eor v2.16b, v2.16b, v10.16b 580 eor v2.16b, v2.16b, v10.16b 608 eor v2.16b, v2.16b, v10.16b 615 eor v2.16b, v2.16b, v10.16b 736 eor v2.16b, v2.16b, v10.16b 747 eor v2.16b, v2.16b, v10.16b [all …]
|
| A D | aes-modes.S | 148 eor v2.16b, v2.16b, v1.16b 200 eor v2.16b, v2.16b, v6.16b 212 eor v2.16b, v2.16b, v5.16b 291 eor v2.16b, v2.16b, v1.16b 464 eor v2.16b, v7.16b, v2.16b 664 eor v2.16b, v2.16b, v6.16b 671 eor v2.16b, v2.16b, v6.16b 718 tbl v2.16b, {v0.16b}, v2.16b 756 eor v2.16b, v2.16b, v6.16b 763 eor v2.16b, v2.16b, v6.16b [all …]
|
| /arch/arm/boot/dts/allwinner/ |
| A D | sun8i-r40-cpu-opp.dtsi | 3 compatible = "operating-points-v2"; 39 operating-points-v2 = <&cpu0_opp_table>; 43 operating-points-v2 = <&cpu0_opp_table>; 47 operating-points-v2 = <&cpu0_opp_table>; 51 operating-points-v2 = <&cpu0_opp_table>;
|
| /arch/arm64/boot/dts/amlogic/ |
| A D | meson-g12b-khadas-vim3.dtsi | 52 operating-points-v2 = <&cpu_opp_table_0>; 58 operating-points-v2 = <&cpu_opp_table_0>; 64 operating-points-v2 = <&cpub_opp_table_1>; 70 operating-points-v2 = <&cpub_opp_table_1>; 76 operating-points-v2 = <&cpub_opp_table_1>; 82 operating-points-v2 = <&cpub_opp_table_1>;
|
| /arch/arm64/boot/dts/allwinner/ |
| A D | sun50i-a64-cpu-opp.dtsi | 8 compatible = "operating-points-v2"; 62 operating-points-v2 = <&cpu0_opp_table>; 66 operating-points-v2 = <&cpu0_opp_table>; 70 operating-points-v2 = <&cpu0_opp_table>; 74 operating-points-v2 = <&cpu0_opp_table>;
|
| A D | sun50i-h5-cpu-opp.dtsi | 6 compatible = "operating-points-v2"; 66 operating-points-v2 = <&cpu_opp_table>; 70 operating-points-v2 = <&cpu_opp_table>; 74 operating-points-v2 = <&cpu_opp_table>; 78 operating-points-v2 = <&cpu_opp_table>;
|
| /arch/arm64/boot/dts/qcom/ |
| A D | sdm660.dtsi | 14 operating-points-v2 = <&gpu_sdm660_opp_table>; 17 compatible = "operating-points-v2"; 91 /delete-property/ operating-points-v2; 97 /delete-property/ operating-points-v2; 103 /delete-property/ operating-points-v2; 109 /delete-property/ operating-points-v2; 115 /delete-property/ operating-points-v2; 121 /delete-property/ operating-points-v2; 127 /delete-property/ operating-points-v2; 133 /delete-property/ operating-points-v2; [all …]
|