Home
last modified time | relevance | path

Searched refs:v2 (Results 1 – 25 of 668) sorted by relevance

12345678910>>...27

/linux/net/ceph/
H A Dmessenger_v2.c114 iov_iter_is_discard(&con->v2.in_iter) ? "discard" : "need", in ceph_tcp_recv()
115 iov_iter_count(&con->v2.in_iter)); in ceph_tcp_recv()
116 ret = do_recvmsg(con->sock, &con->v2.in_iter); in ceph_tcp_recv()
118 iov_iter_count(&con->v2.in_iter)); in ceph_tcp_recv()
201 iov_iter_count(&con->v2.out_iter), con->v2.out_iter_sendpage); in ceph_tcp_send()
202 if (con->v2.out_iter_sendpage) in ceph_tcp_send()
203 ret = do_try_sendpage(con->sock, &con->v2.out_iter); in ceph_tcp_send()
205 ret = do_sendmsg(con->sock, &con->v2.out_iter); in ceph_tcp_send()
207 iov_iter_count(&con->v2.out_iter)); in ceph_tcp_send()
213 BUG_ON(con->v2.in_kvec_cnt >= ARRAY_SIZE(con->v2.in_kvecs)); in add_in_kvec()
[all …]
/linux/arch/loongarch/lib/
H A Dxor_template.c18 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"
52 v2 += LINE_WIDTH / sizeof(unsigned long);
59 const unsigned long * __restrict v2,
68 LD_AND_XOR_LINE(v2)
[all …]
/linux/Documentation/arch/powerpc/
H A Disa-versions.rst14 Power8 Power ISA v2.07
15 e6500 Power ISA v2.06 with some exceptions
16 e5500 Power ISA v2.06 with some exceptions, no Altivec
17 Power7 Power ISA v2.06
18 Power6 Power ISA v2.05
19 PA6T Power ISA v2.04
20 Cell PPU - Power ISA v2.02 with some minor exceptions
22 Power5++ Power ISA v2.04 (no VMX)
23 Power5+ Power ISA v2.03
24 Power5 - PowerPC User Instruction Set Architecture Book I v2.02
[all …]
/linux/arch/arm64/lib/
H A Dxor-neon.c19 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()
48 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
55 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_3()
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()
86 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
93 v2 = veorq_u64(vld1q_u64(dp1 + 4), vld1q_u64(dp2 + 4)); in xor_arm64_neon_4()
99 v2 = veorq_u64(v2, vld1q_u64(dp3 + 4)); in xor_arm64_neon_4()
[all …]
/linux/tools/testing/selftests/powerpc/math/
H A Dvmx_asm.S9 # 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 …]
/linux/include/pcmcia/
H A Ddevice_id.h29 #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 …]
/linux/arch/powerpc/lib/
H A Dxor_vmx.c57 DEFINE(v2); in __xor_altivec_2()
62 LOAD(v2); in __xor_altivec_2()
63 XOR(v1, 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()
85 XOR(v1, 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()
[all …]
/linux/arch/s390/include/asm/
H A Dfpu-insn-asm.h100 .ifc \vxr,%v2
219 .macro RXB rxb v1 v2=0 v3=0 v4=0
224 .if \v2 & 0x10
246 .macro MRXB m v1 v2=0 v3=0 v4=0
248 RXB rxb, \v1, \v2, \v3, \v4
264 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
265 MRXB \m, \v1, \v2, \v3, \v4
308 .macro VLR v1, v2
310 VX_NUM v2, \v2
311 .word 0xE700 | ((v1&15) << 4) | (v2&15)
[all …]
/linux/arch/arm64/boot/dts/rockchip/
H A Drk3588j.dtsi11 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 …]
H A Drk3588-opp.dtsi5 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 …]
H A Drk3399-op1.dtsi10 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 …]
H A Drk3399-t.dtsi11 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>;
H A Drk3399.dtsi10 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>;
/linux/lib/
H A Dxxhash.c96 uint32_t v2 = seed + PRIME32_2; in xxh32() local
103 v2 = xxh32_round(v2, get_unaligned_le32(p)); in xxh32()
111 h32 = xxh_rotl32(v1, 1) + xxh_rotl32(v2, 7) + in xxh32()
166 uint64_t v2 = seed + PRIME64_2; in xxh64() local
173 v2 = xxh64_round(v2, get_unaligned_le64(p)); in xxh64()
181 h64 = xxh_rotl64(v1, 1) + xxh_rotl64(v2, 7) + in xxh64()
184 h64 = xxh64_merge_round(h64, v2); in xxh64()
234 state.v2 = seed + PRIME64_2; in xxh64_reset()
265 state->v2 = xxh64_round(state->v2, get_unaligned_le64(p64)); in xxh64_update()
278 uint64_t v2 = state->v2; in xxh64_update() local
[all …]
/linux/arch/arm64/boot/dts/exynos/
H A Dexynos5433-bus.dtsi14 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 …]
/linux/arch/mips/kernel/
H A Dr4k-bugs64.c44 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 …]
/linux/Documentation/userspace-api/gpio/
H A Dchardev.rst7 This is latest version (v2) of the character device API, as defined in
28 The API is based around two major objects, the :ref:`gpio-v2-chip` and the
29 :ref:`gpio-v2-line-request`.
31 .. _gpio-v2-chip:
43 Lines are requested from the chip using gpio-v2-get-line-ioctl.rst
58 Get Line <gpio-v2-get-line-ioctl>
60 Get Line Info <gpio-v2-get-lineinfo-ioctl>
61 Watch Line Info <gpio-v2-get-lineinfo-watch-ioctl>
63 Read Line Info Changed Events <gpio-v2-lineinfo-changed-read>
65 .. _gpio-v2-line-request:
[all …]
/linux/drivers/gpu/drm/amd/display/dmub/src/
H A Ddmub_reg.h65 #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 …]
/linux/arch/arm64/crypto/
H A Daes-ce-ccm-core.S65 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 …]
H A Dsm3-ce-core.S97 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 …]
H A Dsm4-ce-core.S63 sm4ekey v2.4s, v1.4s, v26.4s;
64 sm4ekey v3.4s, v2.4s, v27.4s;
81 tbl v21.16b, {v2.16b}, v24.16b
124 SM4_CRYPT_BLK8(v0, v1, v2, v3, v4, v5, v6, v7);
140 SM4_CRYPT_BLK4(v0, v1, v2, v3);
183 eor v2.16b, v2.16b, v1.16b
184 SM4_CRYPT_BLK(v2)
185 eor v3.16b, v3.16b, v2.16b
235 rev32 v10.16b, v2.16b
247 eor v11.16b, v11.16b, v2.16b
[all …]
H A Daes-modes.S26 encrypt_block4x v0, v1, v2, v3, w3, x2, x8, w7
31 decrypt_block4x v0, v1, v2, v3, w3, x2, x8, w7
37 encrypt_block5x v0, v1, v2, v3, v4, w3, x2, x8, w7
42 decrypt_block5x v0, v1, v2, v3, v4, w3, x2, x8, w7
148 eor v2.16b, v2.16b, v1.16b
149 encrypt_block v2, w3, x2, x6, w7
150 eor v3.16b, v3.16b, v2.16b
193 mov v7.16b, v2.16b
200 eor v2.16b, v2.16b, v6.16b
206 mov v6.16b, v2.16b
[all …]
/linux/drivers/firmware/google/
H A Dmemconsole-x86-legacy.c39 } __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()
/linux/tools/power/cpupower/debug/kernel/
H A Dcpufreq-test_tsc.c37 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()
/linux/lib/crc/arm64/
H A Dcrc-t10dif-core.S225 CPU_LE( rev64 v2.16b, v2.16b )
233 CPU_LE( ext v2.16b, v2.16b, v2.16b, #8 )
256 fold_32_bytes \p, v2, v3
270 fold_16_bytes \p, v2, v6
319 ld1 {v2.16b}, [x4]
320 tbl v1.16b, {v7.16b}, v2.16b
324 eor v2.16b, v2.16b, v3.16b
325 tbl v3.16b, {v7.16b}, v2.16b
328 sshr v2.16b, v2.16b, #7
332 bsl v2.16b, v1.16b, v0.16b
[all …]

12345678910>>...27