| /Linux-v4.19/lib/raid6/ |
| D | avx2.c | 46 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 …]
|
| D | sse2.c | 45 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 …]
|
| D | avx512.c | 53 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 …]
|
| D | sse1.c | 49 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()
|
| D | mmx.c | 44 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()
|
| D | s390vx.uc | 48 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 …]
|
| D | neon.uc | 61 int d, z, z0;
72 for ( z = z0-1 ; z >= 0 ; z-- ) {
73 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
92 int d, z, z0;
106 for ( z = z0-1 ; z >= start ; z-- ) {
107 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
117 for ( z = start-1 ; z >= 3 ; z -= 4 ) {
125 switch (z) {
|
| D | int.uc | 86 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-- ) {
|
| /Linux-v4.19/drivers/zorro/ |
| D | zorro.c | 54 struct zorro_dev *z; in zorro_find_device() local
59 for (z = from ? from+1 : &zorro_autocon[0]; in zorro_find_device()
60 z < zorro_autocon+zorro_num_autocon; in zorro_find_device()
61 z++) in zorro_find_device()
62 if (id == ZORRO_WILDCARD || id == z->id) in zorro_find_device()
63 return z; in zorro_find_device()
115 struct platform_device *bridge, struct zorro_dev *z) in zorro_find_parent_resource() argument
122 if (zorro_resource_start(z) >= r->start && in zorro_find_parent_resource()
123 zorro_resource_end(z) <= r->end) in zorro_find_parent_resource()
135 struct zorro_dev *z; in amiga_zorro_probe() local
[all …]
|
| D | zorro-sysfs.c | 29 struct zorro_dev *z; \
31 z = to_zorro_dev(dev); \
32 return sprintf(buf, format_string, z->field); \
44 struct zorro_dev *z; in serial_show() local
46 z = to_zorro_dev(dev); in serial_show()
47 return sprintf(buf, "0x%08x\n", be32_to_cpu(z->rom.er_SerialNumber)); in serial_show()
54 struct zorro_dev *z = to_zorro_dev(dev); in resource_show() local
57 (unsigned long)zorro_resource_start(z), in resource_show()
58 (unsigned long)zorro_resource_end(z), in resource_show()
59 zorro_resource_flags(z)); in resource_show()
[all …]
|
| D | zorro-driver.c | 33 const struct zorro_dev *z) in zorro_match_device() argument
36 if (ids->id == ZORRO_WILDCARD || ids->id == z->id) in zorro_match_device()
49 struct zorro_dev *z = to_zorro_dev(dev); in zorro_device_probe() local
51 if (!z->driver && drv->probe) { in zorro_device_probe()
54 id = zorro_match_device(drv->id_table, z); in zorro_device_probe()
56 error = drv->probe(z, id); in zorro_device_probe()
58 z->driver = drv; in zorro_device_probe()
68 struct zorro_dev *z = to_zorro_dev(dev); in zorro_device_remove() local
73 drv->remove(z); in zorro_device_remove()
74 z->driver = NULL; in zorro_device_remove()
[all …]
|
| D | proc.c | 33 struct zorro_dev *z = PDE_DATA(file_inode(file)); in proc_bus_zorro_read() local
46 cd.cd_Rom = z->rom; in proc_bus_zorro_read()
47 cd.cd_SlotAddr = cpu_to_be16(z->slotaddr); in proc_bus_zorro_read()
48 cd.cd_SlotSize = cpu_to_be16(z->slotsize); in proc_bus_zorro_read()
49 cd.cd_BoardAddr = cpu_to_be32(zorro_resource_start(z)); in proc_bus_zorro_read()
50 cd.cd_BoardSize = cpu_to_be32(zorro_resource_len(z)); in proc_bus_zorro_read()
83 struct zorro_dev *z = &zorro_autocon[slot]; in zorro_seq_show() local
85 seq_printf(m, "%02x\t%08x\t%08lx\t%08lx\t%02x\n", slot, z->id, in zorro_seq_show()
86 (unsigned long)zorro_resource_start(z), in zorro_seq_show()
87 (unsigned long)zorro_resource_len(z), in zorro_seq_show()
[all …]
|
| /Linux-v4.19/include/linux/ |
| D | zorro.h | 58 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 …]
|
| D | mmzone.h | 270 #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
753 bool __zone_watermark_ok(struct zone *z, unsigned int order, unsigned long mark,
756 bool zone_watermark_ok(struct zone *z, unsigned int order,
759 bool zone_watermark_ok_safe(struct zone *z, unsigned int order,
964 struct zoneref *__next_zones_zonelist(struct zoneref *z,
980 static __always_inline struct zoneref *next_zones_zonelist(struct zoneref *z, in next_zones_zonelist() argument
984 if (likely(!nodes && zonelist_zone_idx(z) <= highest_zoneidx)) in next_zones_zonelist()
985 return z; in next_zones_zonelist()
[all …]
|
| /Linux-v4.19/crypto/ |
| D | tea.c | 64 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 …]
|
| /Linux-v4.19/drivers/md/ |
| D | dm-zoned.h | 126 #define dmz_is_rnd(z) test_bit(DMZ_RND, &(z)->flags) argument
127 #define dmz_is_seq(z) test_bit(DMZ_SEQ, &(z)->flags) argument
128 #define dmz_is_empty(z) ((z)->wp_block == 0) argument
129 #define dmz_is_offline(z) test_bit(DMZ_OFFLINE, &(z)->flags) argument
130 #define dmz_is_readonly(z) test_bit(DMZ_READ_ONLY, &(z)->flags) argument
131 #define dmz_is_active(z) test_bit(DMZ_ACTIVE, &(z)->flags) argument
132 #define dmz_in_reclaim(z) test_bit(DMZ_RECLAIM, &(z)->flags) argument
133 #define dmz_seq_write_err(z) test_bit(DMZ_SEQ_WRITE_ERR, &(z)->flags) argument
135 #define dmz_is_meta(z) test_bit(DMZ_META, &(z)->flags) argument
136 #define dmz_is_buf(z) test_bit(DMZ_BUF, &(z)->flags) argument
[all …]
|
| /Linux-v4.19/sound/pci/emu10k1/ |
| D | emufx.c | 1198 int err, i, z, gpr, nctl; in _snd_emu10k1_audigy_init_efx() local
1499 for (z = 0; z < 5; z++) { in _snd_emu10k1_audigy_init_efx()
1502 controls[nctl + 0].gpr[z * 2 + j] = BASS_GPR + z * 2 + j; in _snd_emu10k1_audigy_init_efx()
1503 controls[nctl + 1].gpr[z * 2 + j] = TREBLE_GPR + z * 2 + j; in _snd_emu10k1_audigy_init_efx()
1506 for (z = 0; z < 4; z++) { /* front/rear/center-lfe/side */ in _snd_emu10k1_audigy_init_efx()
1509 k = 0xb0 + (z * 8) + (j * 4); in _snd_emu10k1_audigy_init_efx()
1510 l = 0xe0 + (z * 8) + (j * 4); in _snd_emu10k1_audigy_init_efx()
1511 d = playback + SND_EMU10K1_PLAYBACK_CHANNELS + z * 2 + j; in _snd_emu10k1_audigy_init_efx()
1529 if (z == 2) /* center */ in _snd_emu10k1_audigy_init_efx()
1538 for (z = 0; z < 8; z++) { in _snd_emu10k1_audigy_init_efx()
[all …]
|
| /Linux-v4.19/Documentation/devicetree/bindings/iio/accel/ |
| D | lis302.txt | 23 - st,click-single-{x,y,z}: if present, tells the device to issue an
25 x/y/z axis.
26 - st,click-double-{x,y,z}: if present, tells the device to issue an
28 x/y/z axis.
29 - st,click-thresh-{x,y,z}: set the x/y/z axis threshold
47 - st,wakeup-{x,y,z}-{lo,hi}: set wakeup condition on x/y/z axis for
50 - st,wakeup2-{x,y,z}-{lo,hi}: set wakeup condition on x/y/z axis for
59 - st,axis-{x,y,z}=: set the axis to map to the three coordinates.
61 - st,{min,max}-limit-{x,y,z} set the min/max limits for x/y/z axis
76 st,click-single-z;
[all …]
|
| /Linux-v4.19/drivers/net/wan/lmc/ |
| D | lmc_debug.h | 7 #define LMC_CONSOLE_LOG(x,y,z) lmcConsoleLog((x), (y), (z)) argument
9 #define LMC_CONSOLE_LOG(x,y,z) argument
12 #define LMC_CONSOLE_LOG(x,y,z) argument
44 #define LMC_EVENT_LOG(x, y, z) lmcEventLog((x), (y), (z)) argument
46 #define LMC_EVENT_LOG(x,y,z) argument
|
| /Linux-v4.19/drivers/scsi/ |
| D | zorro7xx.c | 74 static int zorro7xx_init_one(struct zorro_dev *z, in zorro7xx_init_one() argument
82 board = zorro_resource_start(z); in zorro7xx_init_one()
91 if (!zorro_request_device(z, zdd->name)) { in zorro7xx_init_one()
105 hostdata->base = ioremap(ioaddr, zorro_resource_len(z)); in zorro7xx_init_one()
119 &z->dev); in zorro7xx_init_one()
136 zorro_set_drvdata(z, host); in zorro7xx_init_one()
148 zorro_release_device(z); in zorro7xx_init_one()
153 static void zorro7xx_remove_one(struct zorro_dev *z) in zorro7xx_remove_one() argument
155 struct Scsi_Host *host = zorro_get_drvdata(z); in zorro7xx_remove_one()
163 zorro_release_device(z); in zorro7xx_remove_one()
|
| /Linux-v4.19/tools/testing/selftests/ftrace/test.d/instances/ |
| D | instance.tc | 11 rmdir x y z 2>/dev/null
35 mkdir z
38 rmdir z
75 mkdir x y z
76 ls x y z
77 rmdir x y z
78 for d in x y z; do
|
| /Linux-v4.19/mm/ |
| D | mmzone.c | 56 struct zoneref *__next_zones_zonelist(struct zoneref *z, in __next_zones_zonelist() argument
65 while (zonelist_zone_idx(z) > highest_zoneidx) in __next_zones_zonelist()
66 z++; in __next_zones_zonelist()
68 while (zonelist_zone_idx(z) > highest_zoneidx || in __next_zones_zonelist()
69 (z->zone && !zref_in_nodemask(z, nodes))) in __next_zones_zonelist()
70 z++; in __next_zones_zonelist()
72 return z; in __next_zones_zonelist()
|
| /Linux-v4.19/drivers/net/ethernet/8390/ |
| D | hydra.c | 56 static int hydra_init_one(struct zorro_dev *z,
58 static int hydra_init(struct zorro_dev *z);
68 static void hydra_remove_one(struct zorro_dev *z);
83 static int hydra_init_one(struct zorro_dev *z, in hydra_init_one() argument
88 if (!request_mem_region(z->resource.start, 0x10000, "Hydra")) in hydra_init_one()
90 if ((err = hydra_init(z))) { in hydra_init_one()
91 release_mem_region(z->resource.start, 0x10000); in hydra_init_one()
112 static int hydra_init(struct zorro_dev *z) in hydra_init() argument
115 unsigned long board = (unsigned long)ZTWO_VADDR(z->resource.start); in hydra_init()
173 zorro_set_drvdata(z, dev); in hydra_init()
[all …]
|
| /Linux-v4.19/arch/arm/nwfpe/ |
| D | softfloat.c | 75 int32 z; in roundAndPackInt32() local
97 z = absZ; in roundAndPackInt32()
98 if ( zSign ) z = - z; in roundAndPackInt32()
99 if ( ( absZ>>32 ) || ( z && ( ( z < 0 ) ^ zSign ) ) ) { in roundAndPackInt32()
104 return z; in roundAndPackInt32()
530 floatx80 z; in packFloatx80() local
532 z.low = zSig; in packFloatx80()
533 z.high = ( ( (bits16) zSign )<<15 ) + zExp; in packFloatx80()
534 z.__padding = 0; in packFloatx80()
535 return z; in packFloatx80()
[all …]
|
| /Linux-v4.19/drivers/video/fbdev/ |
| D | fm2fb.c | 214 static int fm2fb_probe(struct zorro_dev *z, const struct zorro_device_id *id);
229 static int fm2fb_probe(struct zorro_dev *z, const struct zorro_device_id *id) in fm2fb_probe() argument
236 is_fm = z->id == ZORRO_PROD_BSC_FRAMEMASTER_II; in fm2fb_probe()
238 if (!zorro_request_device(z,"fm2fb")) in fm2fb_probe()
241 info = framebuffer_alloc(16 * sizeof(u32), &z->dev); in fm2fb_probe()
243 zorro_release_device(z); in fm2fb_probe()
249 zorro_release_device(z); in fm2fb_probe()
254 fb_fix.smem_start = zorro_resource_start(z); in fm2fb_probe()
289 zorro_release_device(z); in fm2fb_probe()
|
