Home
last modified time | relevance | path

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

123

/linux-4.19.296/lib/raid6/
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()
95 int d, z, z0; in raid6_avx21_xor_syndrome() local
110 for (z = z0-1 ; z >= start ; z--) { in raid6_avx21_xor_syndrome()
116 asm volatile("vmovdqa %0,%%ymm5" :: "m" (dptr[z][d])); in raid6_avx21_xor_syndrome()
121 for (z = start-1 ; z >= 0 ; z--) { in raid6_avx21_xor_syndrome()
153 int d, z, z0; in raid6_avx22_gen_syndrome() local
172 for (z = z0-1; z >= 0; z--) { in raid6_avx22_gen_syndrome()
[all …]
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 …]
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.uc48 static inline void AND(int x, int y, int z)
50 asm volatile ("VN %0,%1,%2" : : "i" (x), "i" (y), "i" (z));
53 static inline void XOR(int x, int y, int z)
55 asm volatile ("VX %0,%1,%2" : : "i" (x), "i" (y), "i" (z));
87 int d, z, z0;
100 for (z = z0 - 1; z >= 0; z--) {
105 LOAD_DATA(16,&dptr[z][d]);
120 int d, z, z0;
134 for (z = z0 - 1; z >= start; z--) {
139 LOAD_DATA(16,&dptr[z][d]);
[all …]
Dneon.uc60 int d, z, z0;
71 for ( z = z0-1 ; z >= 0 ; z-- ) {
72 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
91 int d, z, z0;
105 for ( z = z0-1 ; z >= start ; z-- ) {
106 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
116 for ( z = start-1 ; z >= 3 ; z -= 4 ) {
124 switch (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-- ) {
Dvpermxor.uc48 int d, z, z0;
58 for (z = z0-1; z>=0; z--) {
59 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
Daltivec.uc75 int d, z, z0;
86 for ( z = z0-1 ; z >= 0 ; z-- ) {
87 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
/linux-4.19.296/include/linux/
Dzorro.h58 int (*probe)(struct zorro_dev *z, const struct zorro_device_id *id); /* New device inserted */
59 … void (*remove)(struct zorro_dev *z); /* Device removed (NULL if not a hot-plug capable driver) */
73 … zorro_device_id *zorro_match_device(const struct zorro_device_id *ids, const struct zorro_dev *z);
74 static inline struct zorro_driver *zorro_dev_driver(const struct zorro_dev *z) in zorro_dev_driver() argument
76 return z->driver; in zorro_dev_driver()
107 #define zorro_resource_start(z) ((z)->resource.start) argument
108 #define zorro_resource_end(z) ((z)->resource.end) argument
109 #define zorro_resource_len(z) (resource_size(&(z)->resource)) argument
110 #define zorro_resource_flags(z) ((z)->resource.flags) argument
112 #define zorro_request_device(z, name) \ argument
[all …]
Dmmzone.h270 #define min_wmark_pages(z) (z->watermark[WMARK_MIN]) argument
271 #define low_wmark_pages(z) (z->watermark[WMARK_LOW]) argument
272 #define high_wmark_pages(z) (z->watermark[WMARK_HIGH]) argument
754 bool __zone_watermark_ok(struct zone *z, unsigned int order, unsigned long mark,
757 bool zone_watermark_ok(struct zone *z, unsigned int order,
760 bool zone_watermark_ok_safe(struct zone *z, unsigned int order,
970 struct zoneref *__next_zones_zonelist(struct zoneref *z,
986 static __always_inline struct zoneref *next_zones_zonelist(struct zoneref *z, in next_zones_zonelist() argument
990 if (likely(!nodes && zonelist_zone_idx(z) <= highest_zoneidx)) in next_zones_zonelist()
991 return z; in next_zones_zonelist()
[all …]
Dcpuset.h74 static inline bool __cpuset_zone_allowed(struct zone *z, gfp_t gfp_mask) in __cpuset_zone_allowed() argument
76 return __cpuset_node_allowed(zone_to_nid(z), gfp_mask); in __cpuset_zone_allowed()
79 static inline bool cpuset_zone_allowed(struct zone *z, gfp_t gfp_mask) in cpuset_zone_allowed() argument
82 return __cpuset_zone_allowed(z, gfp_mask); in cpuset_zone_allowed()
207 static inline bool __cpuset_zone_allowed(struct zone *z, gfp_t gfp_mask) in __cpuset_zone_allowed() argument
212 static inline bool cpuset_zone_allowed(struct zone *z, gfp_t gfp_mask) in cpuset_zone_allowed() argument
/linux-4.19.296/crypto/
Dtea.c64 u32 y, z, n, sum = 0; in tea_encrypt() local
71 z = le32_to_cpu(in[1]); in tea_encrypt()
82 y += ((z << 4) + k0) ^ (z + sum) ^ ((z >> 5) + k1); in tea_encrypt()
83 z += ((y << 4) + k2) ^ (y + sum) ^ ((y >> 5) + k3); in tea_encrypt()
87 out[1] = cpu_to_le32(z); in tea_encrypt()
92 u32 y, z, n, sum; in tea_decrypt() local
99 z = le32_to_cpu(in[1]); in tea_decrypt()
111 z -= ((y << 4) + k2) ^ (y + sum) ^ ((y >> 5) + k3); in tea_decrypt()
112 y -= ((z << 4) + k0) ^ (z + sum) ^ ((z >> 5) + k1); in tea_decrypt()
117 out[1] = cpu_to_le32(z); in tea_decrypt()
[all …]
Dcast5_generic.c411 static void key_schedule(u32 *x, u32 *z, u32 *k) in key_schedule() argument
415 #define zi(i) ((z[(i)/4] >> (8*(3-((i)%4)))) & 0xff) in key_schedule()
417 z[0] = x[0] ^ s5[xi(13)] ^ s6[xi(15)] ^ s7[xi(12)] ^ sb8[xi(14)] ^ in key_schedule()
419 z[1] = x[2] ^ s5[zi(0)] ^ s6[zi(2)] ^ s7[zi(1)] ^ sb8[zi(3)] ^ in key_schedule()
421 z[2] = x[3] ^ s5[zi(7)] ^ s6[zi(6)] ^ s7[zi(5)] ^ sb8[zi(4)] ^ in key_schedule()
423 z[3] = x[1] ^ s5[zi(10)] ^ s6[zi(9)] ^ s7[zi(11)] ^ sb8[zi(8)] ^ in key_schedule()
433 x[0] = z[2] ^ s5[zi(5)] ^ s6[zi(7)] ^ s7[zi(4)] ^ sb8[zi(6)] ^ in key_schedule()
435 x[1] = z[0] ^ s5[xi(0)] ^ s6[xi(2)] ^ s7[xi(1)] ^ sb8[xi(3)] ^ in key_schedule()
437 x[2] = z[1] ^ s5[xi(7)] ^ s6[xi(6)] ^ s7[xi(5)] ^ sb8[xi(4)] ^ in key_schedule()
439 x[3] = z[3] ^ s5[xi(10)] ^ s6[xi(9)] ^ s7[xi(11)] ^ sb8[xi(8)] ^ in key_schedule()
[all …]
Dmd5.c35 #define F1(x, y, z) (z ^ (x & (y ^ z))) argument
36 #define F2(x, y, z) F1(z, x, y) argument
37 #define F3(x, y, z) (x ^ y ^ z) argument
38 #define F4(x, y, z) (y ^ (x | ~z)) argument
40 #define MD5STEP(f, w, x, y, z, in, s) \ argument
41 (w += f(x, y, z) + in, w = (w<<s | w>>(32-s)) + x)
Decc.c711 static void apply_z(u64 *x1, u64 *y1, u64 *z, u64 *curve_prime, in apply_z() argument
716 vli_mod_square_fast(t1, z, curve_prime, ndigits); /* z^2 */ in apply_z()
718 vli_mod_mult_fast(t1, t1, z, curve_prime, ndigits); /* z^3 */ in apply_z()
727 u64 z[ECC_MAX_DIGITS]; in xycz_initial_double() local
732 vli_clear(z, ndigits); in xycz_initial_double()
733 z[0] = 1; in xycz_initial_double()
736 vli_set(z, p_initial_z, ndigits); in xycz_initial_double()
738 apply_z(x1, y1, z, curve_prime, ndigits); in xycz_initial_double()
740 ecc_point_double_jacobian(x1, y1, z, curve_prime, ndigits); in xycz_initial_double()
742 apply_z(x2, y2, z, curve_prime, ndigits); in xycz_initial_double()
[all …]
Dmd4.c48 static inline u32 F(u32 x, u32 y, u32 z) in F() argument
50 return (x & y) | ((~x) & z); in F()
53 static inline u32 G(u32 x, u32 y, u32 z) in G() argument
55 return (x & y) | (x & z) | (y & z); in G()
58 static inline u32 H(u32 x, u32 y, u32 z) in H() argument
60 return x ^ y ^ z; in H()
/linux-4.19.296/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
/linux-4.19.296/fs/cachefiles/
Dproc.c27 unsigned x, y, z, t; in cachefiles_histogram_show() local
40 z = atomic_read(&cachefiles_create_histogram[index]); in cachefiles_histogram_show()
41 if (x == 0 && y == 0 && z == 0) in cachefiles_histogram_show()
46 seq_printf(m, "%4lu 0.%03u %9u %9u %9u\n", index, t, x, y, z); in cachefiles_histogram_show()
/linux-4.19.296/drivers/s390/char/
DKconfig161 prompt "Support for the z/VM recording system services (VM only)"
165 by the z/VM recording system services, eg. from *LOGREC, *ACCOUNT or
171 prompt "Support for the z/VM CP interface"
176 program on z/VM
179 int "Memory in MiB reserved for z/VM CP interface"
183 Specify the default amount of memory in MiB reserved for the z/VM CP
190 prompt "API for reading z/VM monitor service records"
193 Character device driver for reading z/VM monitor service records
197 prompt "API for writing z/VM monitor service records"
200 Character device driver for writing z/VM monitor service records
[all …]
/linux-4.19.296/drivers/uwb/
Ddrp-ie.c143 int z, i, num_fields = 0, next = 0; in uwb_drp_ie_from_bm() local
154 for (z = 0; z < UWB_NUM_ZONES; z++) { in uwb_drp_ie_from_bm()
161 zones[i].zone_bm |= 1 << z; in uwb_drp_ie_from_bm()
168 zones[next].zone_bm = 1 << z; in uwb_drp_ie_from_bm()
/linux-4.19.296/fs/ext4/
Dhash.c33 #define F(x, y, z) ((z) ^ ((x) & ((y) ^ (z)))) argument
34 #define G(x, y, z) (((x) & (y)) + (((x) ^ (y)) & (z))) argument
35 #define H(x, y, z) ((x) ^ (y) ^ (z)) argument
/linux-4.19.296/lib/
Dinflate.c351 unsigned z; /* number of entries in current table */ in huft_build() local
450 z = 0; /* ditto */ in huft_build()
470 z = (z = g - w) > (unsigned)l ? l : z; /* upper limit on table size */ in huft_build()
476 if (j < z) in huft_build()
477 while (++j < z) /* try smaller tables up to z bits */ in huft_build()
485 z = 1 << j; /* table entries for j-bit table */ in huft_build()
488 if ((q = (struct huft *)malloc((z + 1)*sizeof(struct huft))) == in huft_build()
497 hufts += z + 1; /* track memory usage */ in huft_build()
536 for (j = i >> w; j < z; j += f) in huft_build()

123