Home
last modified time | relevance | path

Searched full:z0 (Results 1 – 25 of 316) sorted by relevance

12345678910>>...13

/kernel/linux/linux-6.6/tools/testing/selftests/arm64/abi/
Dhwcap.c150 /* BFCLAMP { Z0.H - Z1.H }, Z0.H, Z0.H */ in sme2p1_sigill()
162 /* SMOPA ZA0.S, P0/M, P0/M, Z0.B, Z0.B */ in smei16i32_sigill()
174 /* BMOPA ZA0.S, P0/M, P0/M, Z0.B, Z0.B */ in smebi32i32_sigill()
186 /* BFADD ZA.H[W0, 0], {Z0.H-Z1.H} */ in smeb16b16_sigill()
198 /* FADD ZA.H[W0, 0], { Z0.H-Z1.H } */ in smef16f16_sigill()
213 /* SQABS Z0.b, P0/M, Z0.B */ in sve2_sigill()
214 asm volatile(".inst 0x4408A000" : : : "z0"); in sve2_sigill()
219 /* BFADD Z0.H, Z0.H, Z0.H */ in sve2p1_sigill()
220 asm volatile(".inst 0x65000000" : : : "z0"); in sve2p1_sigill()
225 /* AESD z0.b, z0.b, z0.b */ in sveaes_sigill()
[all …]
/kernel/linux/linux-5.10/lib/raid6/
Dsse1.c44 int d, z, z0; in raid6_sse11_gen_syndrome() local
46 z0 = disks - 3; /* Highest data disk */ in raid6_sse11_gen_syndrome()
47 p = dptr[z0+1]; /* XOR parity */ in raid6_sse11_gen_syndrome()
48 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse11_gen_syndrome()
56 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse11_gen_syndrome()
57 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse11_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
60 asm volatile("movq %0,%%mm6" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
61 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse11_gen_syndrome()
103 int d, z, z0; in raid6_sse12_gen_syndrome() local
[all …]
Dmmx.c39 int d, z, z0; in raid6_mmx1_gen_syndrome() local
41 z0 = disks - 3; /* Highest data disk */ in raid6_mmx1_gen_syndrome()
42 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx1_gen_syndrome()
43 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx1_gen_syndrome()
51 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx1_gen_syndrome()
53 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_mmx1_gen_syndrome()
87 int d, z, z0; in raid6_mmx2_gen_syndrome() local
89 z0 = disks - 3; /* Highest data disk */ in raid6_mmx2_gen_syndrome()
90 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx2_gen_syndrome()
91 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
[all …]
Dsse2.c40 int d, z, z0; in raid6_sse21_gen_syndrome() local
42 z0 = disks - 3; /* Highest data disk */ in raid6_sse21_gen_syndrome()
43 p = dptr[z0+1]; /* XOR parity */ in raid6_sse21_gen_syndrome()
44 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse21_gen_syndrome()
53 asm volatile("movdqa %0,%%xmm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse21_gen_syndrome()
54 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
56 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
57 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse21_gen_syndrome()
92 int d, z, z0; in raid6_sse21_xor_syndrome() local
[all …]
Davx2.c38 int d, z, z0; in raid6_avx21_gen_syndrome() local
40 z0 = disks - 3; /* Highest data disk */ in raid6_avx21_gen_syndrome()
41 p = dptr[z0+1]; /* XOR parity */ in raid6_avx21_gen_syndrome()
42 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
50 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
51 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
54 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
55 for (z = z0-2; z >= 0; z--) { in raid6_avx21_gen_syndrome()
87 int d, z, z0; in raid6_avx21_xor_syndrome() local
[all …]
Davx512.c48 int d, z, z0; in raid6_avx5121_gen_syndrome() local
50 z0 = disks - 3; /* Highest data disk */ in raid6_avx5121_gen_syndrome()
51 p = dptr[z0+1]; /* XOR parity */ in raid6_avx5121_gen_syndrome()
52 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx5121_gen_syndrome()
68 : "m" (dptr[z0][d]), "m" (dptr[z0-1][d])); in raid6_avx5121_gen_syndrome()
69 for (z = z0-2; z >= 0; z--) { in raid6_avx5121_gen_syndrome()
106 int d, z, z0; in raid6_avx5121_xor_syndrome() local
108 z0 = stop; /* P/Q right side optimization */ in raid6_avx5121_xor_syndrome()
122 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
124 for (z = z0-1 ; z >= start ; z--) { in raid6_avx5121_xor_syndrome()
[all …]
Dloongarch_simd.c37 int d, z, z0; in raid6_lsx_gen_syndrome() local
39 z0 = disks - 3; /* Highest data disk */ in raid6_lsx_gen_syndrome()
40 p = dptr[z0+1]; /* XOR parity */ in raid6_lsx_gen_syndrome()
41 q = dptr[z0+2]; /* RS syndrome */ in raid6_lsx_gen_syndrome()
53 /* wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE]; */ in raid6_lsx_gen_syndrome()
54 asm volatile("vld $vr0, %0" : : "m"(dptr[z0][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
55 asm volatile("vld $vr1, %0" : : "m"(dptr[z0][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
56 asm volatile("vld $vr2, %0" : : "m"(dptr[z0][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
57 asm volatile("vld $vr3, %0" : : "m"(dptr[z0][d+3*NSIZE])); in raid6_lsx_gen_syndrome()
62 for (z = z0-1; z >= 0; z--) { in raid6_lsx_gen_syndrome()
[all …]
Dint.uc86 int d, z, z0;
90 z0 = disks - 3; /* Highest data disk */
91 p = dptr[z0+1]; /* XOR parity */
92 q = dptr[z0+2]; /* RS syndrome */
95 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
96 for ( z = z0-1 ; z >= 0 ; z-- ) {
115 int d, z, z0;
119 z0 = stop; /* P/Q right side optimization */
125 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
126 for ( z = z0-1 ; z >= start ; z-- ) {
Ds390vx.uc87 int d, z, z0;
93 z0 = disks - 3; /* Highest data disk */
94 p = dptr[z0 + 1]; /* XOR parity */
95 q = dptr[z0 + 2]; /* RS syndrome */
98 LOAD_DATA(0,&dptr[z0][d]);
100 for (z = z0 - 1; z >= 0; z--) {
120 int d, z, z0;
123 z0 = stop; /* P/Q right side optimization */
132 LOAD_DATA(0,&dptr[z0][d]);
134 for (z = z0 - 1; z >= start; z--) {
Dneon.uc60 int d, z, z0;
65 z0 = disks - 3; /* Highest data disk */
66 p = dptr[z0+1]; /* XOR parity */
67 q = dptr[z0+2]; /* RS syndrome */
70 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
71 for ( z = z0-1 ; z >= 0 ; z-- ) {
91 int d, z, z0;
96 z0 = stop; /* P/Q right side optimization */
101 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
105 for ( z = z0-1 ; z >= start ; z-- ) {
/kernel/linux/linux-6.6/lib/raid6/
Dsse1.c44 int d, z, z0; in raid6_sse11_gen_syndrome() local
46 z0 = disks - 3; /* Highest data disk */ in raid6_sse11_gen_syndrome()
47 p = dptr[z0+1]; /* XOR parity */ in raid6_sse11_gen_syndrome()
48 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse11_gen_syndrome()
56 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse11_gen_syndrome()
57 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse11_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
60 asm volatile("movq %0,%%mm6" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
61 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse11_gen_syndrome()
103 int d, z, z0; in raid6_sse12_gen_syndrome() local
[all …]
Dmmx.c39 int d, z, z0; in raid6_mmx1_gen_syndrome() local
41 z0 = disks - 3; /* Highest data disk */ in raid6_mmx1_gen_syndrome()
42 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx1_gen_syndrome()
43 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx1_gen_syndrome()
51 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx1_gen_syndrome()
53 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_mmx1_gen_syndrome()
87 int d, z, z0; in raid6_mmx2_gen_syndrome() local
89 z0 = disks - 3; /* Highest data disk */ in raid6_mmx2_gen_syndrome()
90 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx2_gen_syndrome()
91 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
[all …]
Dsse2.c40 int d, z, z0; in raid6_sse21_gen_syndrome() local
42 z0 = disks - 3; /* Highest data disk */ in raid6_sse21_gen_syndrome()
43 p = dptr[z0+1]; /* XOR parity */ in raid6_sse21_gen_syndrome()
44 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse21_gen_syndrome()
53 asm volatile("movdqa %0,%%xmm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse21_gen_syndrome()
54 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
56 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
57 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse21_gen_syndrome()
92 int d, z, z0; in raid6_sse21_xor_syndrome() local
[all …]
Davx2.c38 int d, z, z0; in raid6_avx21_gen_syndrome() local
40 z0 = disks - 3; /* Highest data disk */ in raid6_avx21_gen_syndrome()
41 p = dptr[z0+1]; /* XOR parity */ in raid6_avx21_gen_syndrome()
42 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
50 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
51 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
54 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
55 for (z = z0-2; z >= 0; z--) { in raid6_avx21_gen_syndrome()
87 int d, z, z0; in raid6_avx21_xor_syndrome() local
[all …]
Davx512.c48 int d, z, z0; in raid6_avx5121_gen_syndrome() local
50 z0 = disks - 3; /* Highest data disk */ in raid6_avx5121_gen_syndrome()
51 p = dptr[z0+1]; /* XOR parity */ in raid6_avx5121_gen_syndrome()
52 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx5121_gen_syndrome()
68 : "m" (dptr[z0][d]), "m" (dptr[z0-1][d])); in raid6_avx5121_gen_syndrome()
69 for (z = z0-2; z >= 0; z--) { in raid6_avx5121_gen_syndrome()
106 int d, z, z0; in raid6_avx5121_xor_syndrome() local
108 z0 = stop; /* P/Q right side optimization */ in raid6_avx5121_xor_syndrome()
122 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
124 for (z = z0-1 ; z >= start ; z--) { in raid6_avx5121_xor_syndrome()
[all …]
Dloongarch_simd.c37 int d, z, z0; in raid6_lsx_gen_syndrome() local
39 z0 = disks - 3; /* Highest data disk */ in raid6_lsx_gen_syndrome()
40 p = dptr[z0+1]; /* XOR parity */ in raid6_lsx_gen_syndrome()
41 q = dptr[z0+2]; /* RS syndrome */ in raid6_lsx_gen_syndrome()
53 /* wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE]; */ in raid6_lsx_gen_syndrome()
54 asm volatile("vld $vr0, %0" : : "m"(dptr[z0][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
55 asm volatile("vld $vr1, %0" : : "m"(dptr[z0][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
56 asm volatile("vld $vr2, %0" : : "m"(dptr[z0][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
57 asm volatile("vld $vr3, %0" : : "m"(dptr[z0][d+3*NSIZE])); in raid6_lsx_gen_syndrome()
62 for (z = z0-1; z >= 0; z--) { in raid6_lsx_gen_syndrome()
[all …]
Dint.uc86 int d, z, z0;
90 z0 = disks - 3; /* Highest data disk */
91 p = dptr[z0+1]; /* XOR parity */
92 q = dptr[z0+2]; /* RS syndrome */
95 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
96 for ( z = z0-1 ; z >= 0 ; z-- ) {
115 int d, z, z0;
119 z0 = stop; /* P/Q right side optimization */
125 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
126 for ( z = z0-1 ; z >= start ; z-- ) {
Dneon.uc61 int d, z, z0;
66 z0 = disks - 3; /* Highest data disk */
67 p = dptr[z0+1]; /* XOR parity */
68 q = dptr[z0+2]; /* RS syndrome */
71 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
72 for ( z = z0-1 ; z >= 0 ; z-- ) {
92 int d, z, z0;
97 z0 = stop; /* P/Q right side optimization */
102 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
106 for ( z = z0-1 ; z >= start ; z-- ) {
Ds390vx.uc86 int d, z, z0;
92 z0 = disks - 3; /* Highest data disk */
93 p = dptr[z0 + 1]; /* XOR parity */
94 q = dptr[z0 + 2]; /* RS syndrome */
97 LOAD_DATA(0,&dptr[z0][d]);
99 for (z = z0 - 1; z >= 0; z--) {
119 int d, z, z0;
122 z0 = stop; /* P/Q right side optimization */
131 LOAD_DATA(0,&dptr[z0][d]);
133 for (z = z0 - 1; z >= start; z--) {
/kernel/linux/linux-6.6/arch/arm/nwfpe/
Dsoftfloat-macros107 bits64 z0, z1;
112 z0 = a0;
116 z0 = a0>>count;
125 z0 = 0;
128 *z0Ptr = z0;
145 bits64 z0, z1;
150 z0 = a0;
154 z0 = a0>>count;
158 z0 = 0;
161 *z0Ptr = z0;
[all …]
/kernel/linux/linux-5.10/arch/arm/nwfpe/
Dsoftfloat-macros107 bits64 z0, z1;
112 z0 = a0;
116 z0 = a0>>count;
125 z0 = 0;
128 *z0Ptr = z0;
145 bits64 z0, z1;
150 z0 = a0;
154 z0 = a0>>count;
158 z0 = 0;
161 *z0Ptr = z0;
[all …]
/kernel/linux/linux-5.10/arch/arm/boot/dts/
Dkirkwood-rd88f6281-z0.dts3 * Marvell RD88F6181 Z0 stepping descrition
7 * This file contains the definitions for the board using the Z0
16 model = "Marvell RD88f6281 Reference design, with Z0 SoC";
17 …compatible = "marvell,rd88f6281-z0", "marvell,rd88f6281","marvell,kirkwood-88f6281", "marvell,kirk…
/kernel/linux/linux-6.6/arch/arm/boot/dts/marvell/
Dkirkwood-rd88f6281-z0.dts3 * Marvell RD88F6181 Z0 stepping descrition
7 * This file contains the definitions for the board using the Z0
16 model = "Marvell RD88f6281 Reference design, with Z0 SoC";
17 …compatible = "marvell,rd88f6281-z0", "marvell,rd88f6281","marvell,kirkwood-88f6281", "marvell,kirk…
/kernel/linux/linux-6.6/security/apparmor/
DMakefile33 's/^\#define[ \t]+AF_([A-Z0-9_]+)[ \t]+([0-9]+)(.*)/[\2] = "\L\1",/p';\
37 's/^\#define[ \t]+AF_([A-Z0-9_]+)[ \t]+([0-9]+)(.*)/\L\1/p'\
48 -e 's/^\tSOCK_([A-Z0-9_]+)[\t]+=[ \t]+([0-9]+)(.*)/[\2] = "\L\1",/p';\
59 -e 's/^\#define[ \t]+CAP_([A-Z0-9_]+)[ \t]+([0-9]+)/[\2] = "\L\1",/p';\
63 -e 's/^\#define[ \t]+CAP_([A-Z0-9_]+)[ \t]+([0-9]+)/\L\1/p' | \
92 -e 's/^\# ?define[ \t]+(RLIMIT_([A-Z0-9_]+)).*/[\1] = "\L\2",/p';\
95 sed -r -n "s/^\# ?define[ \t]+(RLIMIT_[A-Z0-9_]+).*/\1,/p" $< >> $@ ;\
98 sed -r -n 's/^\# ?define[ \t]+RLIMIT_([A-Z0-9_]+).*/\L\1/p' $< | \
/kernel/linux/linux-5.10/security/apparmor/
DMakefile29 's/^\#define[ \t]+AF_([A-Z0-9_]+)[ \t]+([0-9]+)(.*)/[\2] = "\L\1",/p';\
33 's/^\#define[ \t]+AF_([A-Z0-9_]+)[ \t]+([0-9]+)(.*)/\L\1/p'\
44 -e 's/^\tSOCK_([A-Z0-9_]+)[\t]+=[ \t]+([0-9]+)(.*)/[\2] = "\L\1",/p';\
55 -e 's/^\#define[ \t]+CAP_([A-Z0-9_]+)[ \t]+([0-9]+)/[\2] = "\L\1",/p';\
59 -e 's/^\#define[ \t]+CAP_([A-Z0-9_]+)[ \t]+([0-9]+)/\L\1/p' | \
88 -e 's/^\# ?define[ \t]+(RLIMIT_([A-Z0-9_]+)).*/[\1] = "\L\2",/p';\
91 sed -r -n "s/^\# ?define[ \t]+(RLIMIT_[A-Z0-9_]+).*/\1,/p" $< >> $@ ;\
94 sed -r -n 's/^\# ?define[ \t]+RLIMIT_([A-Z0-9_]+).*/\L\1/p' $< | \

12345678910>>...13