/kernel/linux/linux-5.10/drivers/staging/rtl8723bs/hal/ |
D | HalHWImg8723B_BB.c | 275 u32 v2 = Array[i+1]; in ODM_ReadAndConfig_MP_8723B_AGC_TAB() local 279 odm_ConfigBB_AGC_8723B(pDM_Odm, v1, bMaskDWord, v2); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 288 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 289 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 291 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 292 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 294 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 295 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 299 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() 307 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB() [all …]
|
D | HalHWImg8723B_MAC.c | 246 u32 v2 = Array[i+1]; in ODM_ReadAndConfig_MP_8723B_MAC_REG() local 250 odm_ConfigMAC_8723B(pDM_Odm, v1, (u8)v2); in ODM_ReadAndConfig_MP_8723B_MAC_REG() 259 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG() 260 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_MAC_REG() 262 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG() 263 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG() 265 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG() 266 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_MAC_REG() 270 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG() 276 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG() [all …]
|
D | HalHWImg8723B_RF.c | 277 u32 v2 = Array[i+1]; in ODM_ReadAndConfig_MP_8723B_RadioA() local 281 odm_ConfigRF_RadioA_8723B(pDM_Odm, v1, v2); in ODM_ReadAndConfig_MP_8723B_RadioA() 290 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA() 291 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_RadioA() 293 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA() 294 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA() 296 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA() 297 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_RadioA() 301 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA() 309 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA() [all …]
|
/kernel/linux/linux-5.10/arch/s390/crypto/ |
D | crc32le-vx.S | 132 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE 159 VGFMAG %v2,CONST_R2R1,%v2,%v6 175 VGFMAG %v1,CONST_R4R3,%v1,%v2 184 VL %v2,0,,%r3 /* Load next data chunk */ 185 VPERM %v2,%v2,%v2,CONST_PERM_LE2BE 186 VGFMAG %v1,CONST_R4R3,%v1,%v2 /* Fold next data chunk */ 233 VSRLB %v2,%v1,%v9 /* Store remaining bits in V2 */ 235 VGFMAG %v1,CONST_R5,%v1,%v2 /* V1 = (V1 * R5) XOR V2 */ 257 VUPLLF %v2,%v1 258 VGFMG %v2,CONST_RU_POLY,%v2 [all …]
|
D | crc32be-vx.S | 124 VGFMAG %v2,CONST_R1R2,%v2,%v6 137 VGFMAG %v1,CONST_R3R4,%v1,%v2 147 VL %v2,0,,%r3 /* Load next data chunk */ 148 VGFMAG %v1,CONST_R3R4,%v1,%v2 /* Fold next data chunk */ 196 VUPLLF %v2,%v1 197 VGFMG %v2,CONST_RU_POLY,%v2 204 VUPLLF %v2,%v2 205 VGFMAG %v2,CONST_CRC_POLY,%v2,%v1 208 VLGVF %r2,%v2,3
|
/kernel/linux/linux-5.10/drivers/char/mwave/ |
D | mwavedd.h | 84 #define PRINTK_3(f,s,v1,v2) \ argument 86 printk(s,v1,v2); \ 89 #define PRINTK_4(f,s,v1,v2,v3) \ argument 91 printk(s,v1,v2,v3); \ 94 #define PRINTK_5(f,s,v1,v2,v3,v4) \ argument 96 printk(s,v1,v2,v3,v4); \ 99 #define PRINTK_6(f,s,v1,v2,v3,v4,v5) \ argument 101 printk(s,v1,v2,v3,v4,v5); \ 104 #define PRINTK_7(f,s,v1,v2,v3,v4,v5,v6) \ argument 106 printk(s,v1,v2,v3,v4,v5,v6); \ [all …]
|
/kernel/linux/linux-5.10/tools/testing/selftests/powerpc/math/ |
D | vmx_asm.S | 9 # Should be safe from C, only touches r4, r5 and v0,v1,v2 17 vmr v2,v1 22 vand v2,v2,v1 27 vand v2,v2,v1 32 vand v2,v2,v1 37 vand v2,v2,v1 42 vand v2,v2,v1 47 vand v2,v2,v1 52 vand v2,v2,v1 57 vand v2,v2,v1 [all …]
|
/kernel/linux/linux-5.10/include/pcmcia/ |
D | device_id.h | 29 #define PCMCIA_DEVICE_PROD_ID2(v2, vh2) { \ argument 31 .prod_id = { NULL, (v2), NULL, NULL }, \ 39 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \ argument 42 .prod_id = { (v1), (v2), NULL, NULL }, \ 57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \ argument 61 .prod_id = { (v1), (v2), (v3), NULL },\ 64 #define PCMCIA_DEVICE_PROD_ID124(v1, v2, v4, vh1, vh2, vh4) { \ argument 68 .prod_id = { (v1), (v2), NULL, (v4) }, \ 78 #define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \ argument 83 .prod_id = { (v1), (v2), (v3), (v4) }, \ [all …]
|
/kernel/linux/linux-5.10/arch/arm64/lib/ |
D | xor-neon.c | 19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local 26 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_2() 32 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_2() 47 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local 54 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_3() 60 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_3() 66 vst1q_u64(dp1 + 4, v2); in xor_arm64_neon_3() 83 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local 90 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_4() 96 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_4() [all …]
|
/kernel/linux/linux-5.10/drivers/staging/rtl8188eu/hal/ |
D | rf_cfg.c | 143 #define READ_NEXT_PAIR(v1, v2, i) \ argument 146 v2 = array[i + 1]; \ 192 u32 v2 = array[i + 1]; in rtl88e_phy_config_rf_with_headerfile() local 195 rtl8188e_config_rf_reg(adapt, v1, v2); in rtl88e_phy_config_rf_with_headerfile() 199 READ_NEXT_PAIR(v1, v2, i); in rtl88e_phy_config_rf_with_headerfile() 200 while (v2 != 0xDEAD && v2 != 0xCDEF && in rtl88e_phy_config_rf_with_headerfile() 201 v2 != 0xCDCD && i < array_len - 2) in rtl88e_phy_config_rf_with_headerfile() 202 READ_NEXT_PAIR(v1, v2, i); in rtl88e_phy_config_rf_with_headerfile() 205 READ_NEXT_PAIR(v1, v2, i); in rtl88e_phy_config_rf_with_headerfile() 206 while (v2 != 0xDEAD && v2 != 0xCDEF && in rtl88e_phy_config_rf_with_headerfile() [all …]
|
/kernel/linux/linux-5.10/arch/powerpc/lib/ |
D | xor_vmx.c | 56 DEFINE(v2); in __xor_altivec_2() 61 LOAD(v2); in __xor_altivec_2() 62 XOR(v1, v2); in __xor_altivec_2() 66 v2 += 4; in __xor_altivec_2() 74 DEFINE(v2); in __xor_altivec_3() 80 LOAD(v2); in __xor_altivec_3() 82 XOR(v1, v2); in __xor_altivec_3() 87 v2 += 4; in __xor_altivec_3() 97 DEFINE(v2); in __xor_altivec_4() 104 LOAD(v2); in __xor_altivec_4() [all …]
|
/kernel/linux/linux-5.10/include/linux/ |
D | prandom.h | 30 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument 31 v0 += v1, v1 = rol64(v1, 13), v2 += v3, v3 = rol64(v3, 16), \ 32 v1 ^= v0, v0 = rol64(v0, 32), v3 ^= v2, \ 33 v0 += v3, v3 = rol64(v3, 21), v2 += v1, v1 = rol64(v1, 17), \ 34 v3 ^= v0, v1 ^= v2, v2 = rol64(v2, 32) \ 46 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument 47 v0 += v1, v1 = rol32(v1, 5), v2 += v3, v3 = rol32(v3, 8), \ 48 v1 ^= v0, v0 = rol32(v0, 16), v3 ^= v2, \ 49 v0 += v3, v3 = rol32(v3, 7), v2 += v1, v1 = rol32(v1, 13), \ 50 v3 ^= v0, v1 ^= v2, v2 = rol32(v2, 16) \
|
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dc/inc/ |
D | reg_helper.h | 67 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \ argument 70 FN(reg, f2), v2) 72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \ argument 75 FN(reg, f2), v2,\ 78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \ argument 81 FN(reg, f2), v2,\ 85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument 89 FN(reg, f2), v2,\ 94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument 98 FN(reg, f2), v2,\ [all …]
|
/kernel/linux/linux-5.10/Documentation/powerpc/ |
D | isa-versions.rst | 12 Power8 Power ISA v2.07 13 Power7 Power ISA v2.06 14 Power6 Power ISA v2.05 15 PA6T Power ISA v2.04 16 Cell PPU - Power ISA v2.02 with some minor exceptions 18 Power5++ Power ISA v2.04 (no VMX) 19 Power5+ Power ISA v2.03 20 Power5 - PowerPC User Instruction Set Architecture Book I v2.02 21 - PowerPC Virtual Environment Architecture Book II v2.02 22 - PowerPC Operating Environment Architecture Book III v2.02 [all …]
|
/kernel/linux/linux-5.10/arch/s390/include/asm/ |
D | vx-insn.h | 97 .ifc \vxr,%v2 200 .macro RXB rxb v1 v2=0 v3=0 v4=0 205 .if \v2 & 0x10 224 .macro MRXB m v1 v2=0 v3=0 v4=0 226 RXB rxb, \v1, \v2, \v3, \v4 239 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0 240 MRXB \m, \v1, \v2, \v3, \v4 283 .macro VLR v1, v2 285 VX_NUM v2, \v2 286 .word 0xE700 | ((v1&15) << 4) | (v2&15) [all …]
|
/kernel/linux/linux-5.10/lib/ |
D | random32.c | 336 unsigned long v2; member 365 unsigned long v0 = s->v0, v1 = s->v1, v2 = s->v2, v3 = s->v3; in siprand_u32() local 369 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32() 370 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32() 372 s->v0 = v0; s->v1 = v1; s->v2 = v2; s->v3 = v3; in siprand_u32() 441 unsigned long v2 = state->v2, v3 = state->v3; in prandom_seed() local 445 PRND_SIPROUND(v0, v1, v2, v3); in prandom_seed() 446 PRND_SIPROUND(v0, v1, v2, v3); in prandom_seed() 448 } while (unlikely(!v0 || !v1 || !v2 || !v3)); in prandom_seed() 452 WRITE_ONCE(state->v2, v2); in prandom_seed() [all …]
|
D | xxhash.c | 111 uint32_t v2 = seed + PRIME32_2; in xxh32() local 118 v2 = xxh32_round(v2, get_unaligned_le32(p)); in xxh32() 126 h32 = xxh_rotl32(v1, 1) + xxh_rotl32(v2, 7) + in xxh32() 181 uint64_t v2 = seed + PRIME64_2; in xxh64() local 188 v2 = xxh64_round(v2, get_unaligned_le64(p)); in xxh64() 196 h64 = xxh_rotl64(v1, 1) + xxh_rotl64(v2, 7) + in xxh64() 199 h64 = xxh64_merge_round(h64, v2); in xxh64() 249 state.v2 = seed + PRIME32_2; in xxh32_reset() 263 state.v2 = seed + PRIME64_2; in xxh64_reset() 295 state->v2 = xxh32_round(state->v2, get_unaligned_le32(p32)); in xxh32_update() [all …]
|
/kernel/linux/linux-5.10/arch/mips/kernel/ |
D | r4k-bugs64.c | 43 void mult_sh_align_mod(long *v1, long *v2, long *w, in mult_sh_align_mod() argument 114 *v2 = lv2; in mult_sh_align_mod() 120 long v1[8], v2[8], w[8]; in check_mult_sh() local 134 mult_sh_align_mod(&v1[0], &v2[0], &w[0], 32, 0); in check_mult_sh() 135 mult_sh_align_mod(&v1[1], &v2[1], &w[1], 32, 1); in check_mult_sh() 136 mult_sh_align_mod(&v1[2], &v2[2], &w[2], 32, 2); in check_mult_sh() 137 mult_sh_align_mod(&v1[3], &v2[3], &w[3], 32, 3); in check_mult_sh() 138 mult_sh_align_mod(&v1[4], &v2[4], &w[4], 32, 4); in check_mult_sh() 139 mult_sh_align_mod(&v1[5], &v2[5], &w[5], 32, 5); in check_mult_sh() 140 mult_sh_align_mod(&v1[6], &v2[6], &w[6], 32, 6); in check_mult_sh() [all …]
|
/kernel/linux/linux-5.10/arch/arm64/boot/dts/exynos/ |
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>; 46 operating-points-v2 = <&bus_g2d_400_opp_table>; 54 operating-points-v2 = <&bus_g2d_400_opp_table>; 62 operating-points-v2 = <&bus_g2d_400_opp_table>; 70 operating-points-v2 = <&bus_hevc_opp_table>; 78 operating-points-v2 = <&bus_hevc_opp_table>; 86 operating-points-v2 = <&bus_noc2_opp_table>; [all …]
|
/kernel/linux/linux-5.10/arch/arm64/boot/dts/rockchip/ |
D | rk3399-opp.dtsi | 8 compatible = "operating-points-v2"; 39 compatible = "operating-points-v2"; 78 compatible = "operating-points-v2"; 108 operating-points-v2 = <&cluster0_opp>; 112 operating-points-v2 = <&cluster0_opp>; 116 operating-points-v2 = <&cluster0_opp>; 120 operating-points-v2 = <&cluster0_opp>; 124 operating-points-v2 = <&cluster1_opp>; 128 operating-points-v2 = <&cluster1_opp>; 132 operating-points-v2 = <&gpu_opp_table>;
|
D | rk3399-op1-opp.dtsi | 8 compatible = "operating-points-v2"; 43 compatible = "operating-points-v2"; 86 compatible = "operating-points-v2"; 116 operating-points-v2 = <&cluster0_opp>; 120 operating-points-v2 = <&cluster0_opp>; 124 operating-points-v2 = <&cluster0_opp>; 128 operating-points-v2 = <&cluster0_opp>; 132 operating-points-v2 = <&cluster1_opp>; 136 operating-points-v2 = <&cluster1_opp>; 140 operating-points-v2 = <&gpu_opp_table>;
|
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dmub/src/ |
D | dmub_reg.h | 65 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \ argument 68 FN(reg, f2), v2) 70 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \ argument 73 FN(reg, f2), v2, \ 76 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \ argument 79 FN(reg, f2), v2, \ 92 #define REG_UPDATE_2(reg, f1, v1, f2, v2) \ argument 95 FN(reg, f2), v2) 97 #define REG_UPDATE_3(reg, f1, v1, f2, v2, f3, v3) \ argument 100 FN(reg, f2), v2, \ [all …]
|
/kernel/linux/linux-5.10/drivers/firmware/google/ |
D | memconsole-x86-legacy.c | 39 } __packed v2; member 70 hdr->v2.buffer_addr, hdr->v2.start, in found_v2_header() 71 hdr->v2.end, hdr->v2.num_bytes); in found_v2_header() 73 memconsole_baseaddr = phys_to_virt(hdr->v2.buffer_addr + hdr->v2.start); in found_v2_header() 74 memconsole_length = hdr->v2.end - hdr->v2.start; in found_v2_header()
|
/kernel/linux/linux-5.10/tools/power/cpupower/debug/kernel/ |
D | cpufreq-test_tsc.c | 37 u32 v1=0,v2=0,v3=0; in read_pmtmr() local 45 v2 = inl(pm_tmr_ioport); in read_pmtmr() 47 } while ((v1 > v2 && v1 < v3) || (v2 > v3 && v2 < v1) in read_pmtmr() 48 || (v3 > v1 && v3 < v2)); in read_pmtmr() 51 return (v2 & 0xFFFFFF); in read_pmtmr()
|
/kernel/linux/linux-5.10/arch/arm64/crypto/ |
D | sm3-ce-core.S | 96 CPU_LE( rev32 v2.16b, v2.16b ) 101 qround a, v0, v1, v2, v3, v4 102 qround a, v1, v2, v3, v4, v0 103 qround a, v2, v3, v4, v0, v1 104 qround a, v3, v4, v0, v1, v2 108 qround b, v4, v0, v1, v2, v3 109 qround b, v0, v1, v2, v3, v4 110 qround b, v1, v2, v3, v4, v0 111 qround b, v2, v3, v4, v0, v1 112 qround b, v3, v4, v0, v1, v2 [all …]
|