Home
last modified time | relevance | path

Searched refs:z (Results 1 – 17 of 17) sorted by relevance

/lib/raid6/
Dsse2.c45 int d, z, z0; in raid6_sse21_gen_syndrome() local
62 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse21_gen_syndrome()
63 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
71 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
97 int d, z, z0; in raid6_sse21_xor_syndrome() local
112 for ( z = z0-1 ; z >= start ; z-- ) { in raid6_sse21_xor_syndrome()
118 asm volatile("movdqa %0,%%xmm5" :: "m" (dptr[z][d])); in raid6_sse21_xor_syndrome()
123 for ( z = start-1 ; z >= 0 ; z-- ) { in raid6_sse21_xor_syndrome()
155 int d, z, z0; in raid6_sse22_gen_syndrome() local
174 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_sse22_gen_syndrome()
[all …]
Davx512.c53 int d, z, z0; in raid6_avx5121_gen_syndrome() local
74 for (z = z0-2; z >= 0; z--) { in raid6_avx5121_gen_syndrome()
85 : "m" (dptr[z][d])); in raid6_avx5121_gen_syndrome()
111 int d, z, z0; in raid6_avx5121_xor_syndrome() local
129 for (z = z0-1 ; z >= start ; z--) { in raid6_avx5121_xor_syndrome()
140 : "m" (dptr[z][d])); in raid6_avx5121_xor_syndrome()
143 for (z = start-1 ; z >= 0 ; z--) { in raid6_avx5121_xor_syndrome()
180 int d, z, z0; in raid6_avx5122_gen_syndrome() local
203 for (z = z0-1; z >= 0; z--) { in raid6_avx5122_gen_syndrome()
223 : "m" (dptr[z][d]), "m" (dptr[z][d+64])); in raid6_avx5122_gen_syndrome()
[all …]
Davx2.c46 int d, z, z0; in raid6_avx21_gen_syndrome() local
63 for (z = z0-2; z >= 0; z--) { in raid6_avx21_gen_syndrome()
64 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
71 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
105 int d, z, z0; in raid6_avx22_gen_syndrome() local
124 for (z = z0-1; z >= 0; z--) { in raid6_avx22_gen_syndrome()
125 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_avx22_gen_syndrome()
126 asm volatile("prefetchnta %0" : : "m" (dptr[z][d+32])); in raid6_avx22_gen_syndrome()
135 asm volatile("vmovdqa %0,%%ymm5" : : "m" (dptr[z][d])); in raid6_avx22_gen_syndrome()
136 asm volatile("vmovdqa %0,%%ymm7" : : "m" (dptr[z][d+32])); in raid6_avx22_gen_syndrome()
[all …]
Dsse1.c49 int d, z, z0; in raid6_sse11_gen_syndrome() local
66 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse11_gen_syndrome()
67 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
75 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
108 int d, z, z0; in raid6_sse12_gen_syndrome() local
127 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_sse12_gen_syndrome()
128 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse12_gen_syndrome()
137 asm volatile("movq %0,%%mm5" : : "m" (dptr[z][d])); in raid6_sse12_gen_syndrome()
138 asm volatile("movq %0,%%mm7" : : "m" (dptr[z][d+8])); in raid6_sse12_gen_syndrome()
Dmmx.c44 int d, z, z0; in raid6_mmx1_gen_syndrome() local
58 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_mmx1_gen_syndrome()
59 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_mmx1_gen_syndrome()
92 int d, z, z0; in raid6_mmx2_gen_syndrome() local
109 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_mmx2_gen_syndrome()
118 asm volatile("movq %0,%%mm5" : : "m" (dptr[z][d])); in raid6_mmx2_gen_syndrome()
119 asm volatile("movq %0,%%mm7" : : "m" (dptr[z][d+8])); in raid6_mmx2_gen_syndrome()
Ds390vx.uc47 static inline void AND(int x, int y, int z)
49 asm volatile ("VN %0,%1,%2" : : "i" (x), "i" (y), "i" (z));
52 static inline void XOR(int x, int y, int z)
54 asm volatile ("VX %0,%1,%2" : : "i" (x), "i" (y), "i" (z));
84 int d, z, z0;
97 for (z = z0 - 1; z >= 0; z--) {
102 LOAD_DATA(16,$#,&dptr[z][d]);
117 int d, z, z0;
131 for (z = z0 - 1; z >= start; z--) {
136 LOAD_DATA(16,$#,&dptr[z][d]);
[all …]
Dneon.uc57 int d, z, z0;
68 for ( z = z0-1 ; z >= 0 ; z-- ) {
69 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
88 int d, z, z0;
102 for ( z = z0-1 ; z >= start ; z-- ) {
103 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
113 for ( z = start-1 ; z >= 0 ; z-- ) {
Dint.uc86 int d, z, z0;
96 for ( z = z0-1 ; z >= 0 ; z-- ) {
97 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
115 int d, z, z0;
126 for ( z = z0-1 ; z >= start ; z-- ) {
127 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
136 for ( z = start-1 ; z >= 0 ; z-- ) {
Dtilegx.uc54 int d, z, z0;
67 for ( z = z0-1 ; z >= 0 ; z-- ) {
68 wd$$ = *(u64 *)&dptr[z][d+$$*NSIZE];
Daltivec.uc72 int d, z, z0;
83 for ( z = z0-1 ; z >= 0 ; z-- ) {
84 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
/lib/
Dhalfmd4.c7 #define F(x, y, z) ((z) ^ ((x) & ((y) ^ (z)))) argument
8 #define G(x, y, z) (((x) & (y)) + (((x) ^ (y)) & (z))) argument
9 #define H(x, y, z) ((x) ^ (y) ^ (z)) argument
Dmd5.c5 #define F1(x, y, z) (z ^ (x & (y ^ z))) argument
6 #define F2(x, y, z) F1(z, x, y) argument
7 #define F3(x, y, z) (x ^ y ^ z) argument
8 #define F4(x, y, z) (y ^ (x | ~z)) argument
10 #define MD5STEP(f, w, x, y, z, in, s) \ argument
11 (w += f(x, y, z) + in, w = (w<<s | w>>(32-s)) + x)
Dinflate.c350 unsigned z; /* number of entries in current table */ in huft_build() local
449 z = 0; /* ditto */ in huft_build()
469 z = (z = g - w) > (unsigned)l ? l : z; /* upper limit on table size */ in huft_build()
475 if (j < z) in huft_build()
476 while (++j < z) /* try smaller tables up to z bits */ in huft_build()
484 z = 1 << j; /* table entries for j-bit table */ in huft_build()
487 if ((q = (struct huft *)malloc((z + 1)*sizeof(struct huft))) == in huft_build()
496 hufts += z + 1; /* track memory usage */ in huft_build()
535 for (j = i >> w; j < z; j += f) in huft_build()
Dbch.c796 const struct gf_poly *f, struct gf_poly *z, in compute_trace_bk_mod() argument
803 z->deg = 1; in compute_trace_bk_mod()
804 z->c[0] = 0; in compute_trace_bk_mod()
805 z->c[1] = bch->a_pow_tab[k]; in compute_trace_bk_mod()
815 for (j = z->deg; j >= 0; j--) { in compute_trace_bk_mod()
816 out->c[j] ^= z->c[j]; in compute_trace_bk_mod()
817 z->c[2*j] = gf_sqr(bch, z->c[j]); in compute_trace_bk_mod()
818 z->c[2*j+1] = 0; in compute_trace_bk_mod()
820 if (z->deg > out->deg) in compute_trace_bk_mod()
821 out->deg = z->deg; in compute_trace_bk_mod()
[all …]
/lib/zlib_inflate/
Dinflate.c757 int zlib_inflateIncomp(z_stream *z) in zlib_inflateIncomp() argument
759 struct inflate_state *state = (struct inflate_state *)z->state; in zlib_inflateIncomp()
760 Byte *saved_no = z->next_out; in zlib_inflateIncomp()
761 uInt saved_ao = z->avail_out; in zlib_inflateIncomp()
767 z->avail_out = 0; in zlib_inflateIncomp()
768 z->next_out = (unsigned char*)z->next_in + z->avail_in; in zlib_inflateIncomp()
770 zlib_updatewindow(z, z->avail_in); in zlib_inflateIncomp()
773 z->avail_out = saved_ao; in zlib_inflateIncomp()
774 z->next_out = saved_no; in zlib_inflateIncomp()
776 z->adler = state->check = in zlib_inflateIncomp()
[all …]
Dinfutil.h23 #define WS(z) ((struct inflate_workspace *)(z->workspace)) argument
/lib/mpi/
Dmpicoder.c334 int x, j, z, lzeros, ents; in mpi_read_raw_from_sgl() local
395 z = BYTES_PER_MPI_LIMB - nbytes % BYTES_PER_MPI_LIMB; in mpi_read_raw_from_sgl()
396 z %= BYTES_PER_MPI_LIMB; in mpi_read_raw_from_sgl()
405 if (((z + x + 1) % BYTES_PER_MPI_LIMB) == 0) { in mpi_read_raw_from_sgl()
410 z += x; in mpi_read_raw_from_sgl()