Home
last modified time | relevance | path

Searched refs:wd (Results 1 – 25 of 46) sorted by relevance

12

/Linux-v4.19/drivers/scsi/
Dwd719x.c49 static inline u8 wd719x_readb(struct wd719x *wd, u8 reg) in wd719x_readb() argument
51 return ioread8(wd->base + reg); in wd719x_readb()
54 static inline u32 wd719x_readl(struct wd719x *wd, u8 reg) in wd719x_readl() argument
56 return ioread32(wd->base + reg); in wd719x_readl()
59 static inline void wd719x_writeb(struct wd719x *wd, u8 reg, u8 val) in wd719x_writeb() argument
61 iowrite8(val, wd->base + reg); in wd719x_writeb()
64 static inline void wd719x_writew(struct wd719x *wd, u8 reg, u16 val) in wd719x_writew() argument
66 iowrite16(val, wd->base + reg); in wd719x_writew()
69 static inline void wd719x_writel(struct wd719x *wd, u8 reg, u32 val) in wd719x_writel() argument
71 iowrite32(val, wd->base + reg); in wd719x_writel()
[all …]
/Linux-v4.19/sound/soc/au1x/
Dpsc-i2s.c299 struct au1xpsc_audio_data *wd; in au1xpsc_i2s_drvprobe() local
301 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_i2s_drvprobe()
303 if (!wd) in au1xpsc_i2s_drvprobe()
307 wd->mmio = devm_ioremap_resource(&pdev->dev, iores); in au1xpsc_i2s_drvprobe()
308 if (IS_ERR(wd->mmio)) in au1xpsc_i2s_drvprobe()
309 return PTR_ERR(wd->mmio); in au1xpsc_i2s_drvprobe()
314 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_i2s_drvprobe()
319 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_i2s_drvprobe()
324 sel = __raw_readl(PSC_SEL(wd)) & PSC_SEL_CLK_MASK; in au1xpsc_i2s_drvprobe()
325 __raw_writel(PSC_CTRL_DISABLE, PSC_CTRL(wd)); in au1xpsc_i2s_drvprobe()
[all …]
Dpsc-ac97.c372 struct au1xpsc_audio_data *wd; in au1xpsc_ac97_drvprobe() local
374 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_ac97_drvprobe()
376 if (!wd) in au1xpsc_ac97_drvprobe()
379 mutex_init(&wd->lock); in au1xpsc_ac97_drvprobe()
382 wd->mmio = devm_ioremap_resource(&pdev->dev, iores); in au1xpsc_ac97_drvprobe()
383 if (IS_ERR(wd->mmio)) in au1xpsc_ac97_drvprobe()
384 return PTR_ERR(wd->mmio); in au1xpsc_ac97_drvprobe()
389 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_ac97_drvprobe()
394 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_ac97_drvprobe()
397 wd->cfg = PSC_AC97CFG_RT_FIFO8 | PSC_AC97CFG_TT_FIFO8 | in au1xpsc_ac97_drvprobe()
[all …]
/Linux-v4.19/arch/mips/include/asm/
Dasmmacro.h260 .macro ld_b wd, off, base
265 ld.b $w\wd, \off(\base)
269 .macro ld_h wd, off, base
274 ld.h $w\wd, \off(\base)
278 .macro ld_w wd, off, base
283 ld.w $w\wd, \off(\base)
287 .macro ld_d wd, off, base
292 ld.d $w\wd, \off(\base)
296 .macro st_b wd, off, base
301 st.b $w\wd, \off(\base)
[all …]
/Linux-v4.19/fs/hfsplus/
Dwrapper.c95 static int hfsplus_read_mdb(void *bufptr, struct hfsplus_wd *wd) in hfsplus_read_mdb() argument
111 wd->ablk_size = in hfsplus_read_mdb()
113 if (wd->ablk_size < HFSPLUS_SECTOR_SIZE) in hfsplus_read_mdb()
115 if (wd->ablk_size % HFSPLUS_SECTOR_SIZE) in hfsplus_read_mdb()
117 wd->ablk_start = in hfsplus_read_mdb()
121 wd->embed_start = (extent >> 16) & 0xFFFF; in hfsplus_read_mdb()
122 wd->embed_count = extent & 0xFFFF; in hfsplus_read_mdb()
163 struct hfsplus_wd wd; in hfsplus_read_wrapper() local
199 if (!hfsplus_read_mdb(sbi->s_vhdr, &wd)) in hfsplus_read_wrapper()
201 wd.ablk_size >>= HFSPLUS_SECTOR_SHIFT; in hfsplus_read_wrapper()
[all …]
/Linux-v4.19/drivers/acpi/arm64/
Dgtdt.c67 struct acpi_gtdt_watchdog *wd = platform_timer; in is_non_secure_watchdog() local
72 return !(wd->timer_flags & ACPI_GTDT_WATCHDOG_SECURE); in is_non_secure_watchdog()
331 static int __init gtdt_import_sbsa_gwdt(struct acpi_gtdt_watchdog *wd, in gtdt_import_sbsa_gwdt() argument
335 int irq = map_gt_gsi(wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
342 DEFINE_RES_MEM(wd->control_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
343 DEFINE_RES_MEM(wd->refresh_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
349 wd->refresh_frame_address, wd->control_frame_address, in gtdt_import_sbsa_gwdt()
350 wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
352 if (!(wd->refresh_frame_address && wd->control_frame_address)) { in gtdt_import_sbsa_gwdt()
354 acpi_unregister_gsi(wd->timer_interrupt); in gtdt_import_sbsa_gwdt()
[all …]
/Linux-v4.19/fs/notify/inotify/
Dinotify_user.c193 inotify_event.wd = event->wd; in copy_event_to_user()
370 i_mark->wd = ret; in inotify_add_to_idr()
380 int wd) in inotify_idr_find_locked() argument
388 i_mark = idr_find(idr, wd); in inotify_idr_find_locked()
401 int wd) in inotify_idr_find() argument
407 i_mark = inotify_idr_find_locked(group, wd); in inotify_idr_find()
423 int wd; in inotify_remove_from_idr() local
426 wd = i_mark->wd; in inotify_remove_from_idr()
432 if (wd == -1) { in inotify_remove_from_idr()
434 __func__, i_mark, i_mark->wd, i_mark->fsn_mark.group); in inotify_remove_from_idr()
[all …]
Dinotify.h8 int wd; member
16 int wd; member
Dinotify_fsnotify.c118 event->wd = i_mark->wd; in inotify_handle_event()
172 fsn_mark->group, i_mark->wd); in idr_callback()
/Linux-v4.19/drivers/watchdog/
Dintel-mid_wdt.c44 static int wdt_start(struct watchdog_device *wd) in wdt_start() argument
46 struct device *dev = watchdog_get_drvdata(wd); in wdt_start()
48 int timeout = wd->timeout; in wdt_start()
67 static int wdt_ping(struct watchdog_device *wd) in wdt_ping() argument
69 struct device *dev = watchdog_get_drvdata(wd); in wdt_ping()
79 static int wdt_stop(struct watchdog_device *wd) in wdt_stop() argument
81 struct device *dev = watchdog_get_drvdata(wd); in wdt_stop()
Dxen_wdt.c125 struct sched_watchdog wd = { .id = ~0 }; in xen_wdt_probe() local
126 int ret = HYPERVISOR_sched_op(SCHEDOP_watchdog, &wd); in xen_wdt_probe()
/Linux-v4.19/drivers/hid/
Dhid-logitech-hidpp.c1518 struct hidpp_ff_work_data *wd = container_of(w, struct hidpp_ff_work_data, work); in hidpp_ff_work_handler() local
1519 struct hidpp_ff_private_data *data = wd->data; in hidpp_ff_work_handler()
1525 switch (wd->effect_id) { in hidpp_ff_work_handler()
1527 wd->params[0] = data->slot_autocenter; in hidpp_ff_work_handler()
1534 wd->params[0] = hidpp_ff_find_effect(data, wd->effect_id); in hidpp_ff_work_handler()
1540 wd->command, wd->params, wd->size, &response); in hidpp_ff_work_handler()
1548 switch (wd->command) { in hidpp_ff_work_handler()
1552 if (wd->effect_id >= 0) in hidpp_ff_work_handler()
1554 data->effect_ids[slot-1] = wd->effect_id; in hidpp_ff_work_handler()
1555 else if (wd->effect_id >= HIDPP_FF_EFFECTID_AUTOCENTER) in hidpp_ff_work_handler()
[all …]
/Linux-v4.19/include/net/
Dpkt_sched.h75 void qdisc_watchdog_init_clockid(struct qdisc_watchdog *wd, struct Qdisc *qdisc,
77 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc);
78 void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, u64 expires);
80 static inline void qdisc_watchdog_schedule(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule() argument
83 qdisc_watchdog_schedule_ns(wd, PSCHED_TICKS2NS(expires)); in qdisc_watchdog_schedule()
86 void qdisc_watchdog_cancel(struct qdisc_watchdog *wd);
/Linux-v4.19/drivers/pinctrl/zte/
Dpinctrl-zx.h54 #define TOP_PIN(pin, off, bp, wd, coff, cbp, ...) { \ argument
61 .width = wd, \
69 #define AON_PIN(pin, off, bp, wd, coff, cbp, ...) { \ argument
76 .width = wd, \
/Linux-v4.19/lib/raid6/
Dint.uc88 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
97 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
98 wp$$ ^= wd$$;
103 wq$$ = w1$$ ^ wd$$;
117 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
127 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
128 wp$$ ^= wd$$;
133 wq$$ = w1$$ ^ wd$$;
Dneon.uc63 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
73 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
74 wp$$ = veorq_u8(wp$$, wd$$);
80 wq$$ = veorq_u8(w1$$, wd$$);
94 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
107 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
108 wp$$ = veorq_u8(wp$$, wd$$);
114 wq$$ = veorq_u8(w1$$, wd$$);
Dvpermxor.uc49 unative_t wp$$, wq$$, wd$$;
59 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
61 wp$$ = vec_xor(wp$$, wd$$);
65 wq$$ = vec_xor(wq$$, wd$$);
Daltivec.uc77 unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
87 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
88 wp$$ = vec_xor(wp$$, wd$$);
93 wq$$ = vec_xor(w1$$, wd$$);
/Linux-v4.19/Documentation/devicetree/bindings/gpio/
Dwd,mbl-gpio.txt8 - compatible: should be "wd,mbl-gpio"
24 compatible = "wd,mbl-gpio";
32 compatible = "wd,mbl-gpio";
/Linux-v4.19/Documentation/core-api/
Derrseq.rst71 struct worker_drone wd;
73 wd.wd_err = (errseq_t)0;
85 su.s_wd_err = errseq_sample(&wd.wd_err);
93 err = errseq_check_and_advance(&wd.wd_err, &su.s_wd_err);
103 errseq_set(&wd.wd_err, -EIO);
122 errseq_t since = errseq_sample(&wd.wd_err);
124 err = errseq_check(&wd.wd_err, since);
146 if (errseq_check(&wd.wd_err, READ_ONCE(su.s_wd_err)) {
149 err = errseq_check_and_advance(&wd.wd_err, &su.s_wd_err);
/Linux-v4.19/drivers/base/power/
Dmain.c466 #define DECLARE_DPM_WATCHDOG_ON_STACK(wd) \ argument
467 struct dpm_watchdog wd
479 struct dpm_watchdog *wd = from_timer(wd, t, timer); in dpm_watchdog_handler() local
481 dev_emerg(wd->dev, "**** DPM device timeout ****\n"); in dpm_watchdog_handler()
482 show_stack(wd->tsk, NULL); in dpm_watchdog_handler()
484 dev_driver_string(wd->dev), dev_name(wd->dev)); in dpm_watchdog_handler()
492 static void dpm_watchdog_set(struct dpm_watchdog *wd, struct device *dev) in dpm_watchdog_set() argument
494 struct timer_list *timer = &wd->timer; in dpm_watchdog_set()
496 wd->dev = dev; in dpm_watchdog_set()
497 wd->tsk = current; in dpm_watchdog_set()
[all …]
/Linux-v4.19/arch/arm/boot/dts/
Dox810se-wd-mbwe.dts2 * wd-mbwe.dtsi - Device tree file for Western Digital My Book World Edition
15 compatible = "wd,mbwe", "oxsemi,ox810se";
/Linux-v4.19/drivers/net/ethernet/qlogic/qlcnic/
Dqlcnic_hw.c32 u32 wd[4]; member
1309 ms->wd[0] = QLCNIC_MS_WRTDATA_LO; in qlcnic_set_ms_controls()
1311 ms->wd[1] = QLCNIC_MS_WRTDATA_HI; in qlcnic_set_ms_controls()
1313 ms->wd[2] = QLCNIC_MS_WRTDATA_ULO; in qlcnic_set_ms_controls()
1314 ms->wd[3] = QLCNIC_MS_WRTDATA_UHI; in qlcnic_set_ms_controls()
1318 ms->wd[0] = QLCNIC_MS_WRTDATA_ULO; in qlcnic_set_ms_controls()
1320 ms->wd[1] = QLCNIC_MS_WRTDATA_UHI; in qlcnic_set_ms_controls()
1322 ms->wd[2] = QLCNIC_MS_WRTDATA_LO; in qlcnic_set_ms_controls()
1323 ms->wd[3] = QLCNIC_MS_WRTDATA_HI; in qlcnic_set_ms_controls()
1377 qlcnic_ind_wr(adapter, ms.wd[0], qlcnic_ind_rd(adapter, ms.rd[0])); in qlcnic_pci_mem_write_2M()
[all …]
/Linux-v4.19/net/sched/
Dsch_api.c589 struct qdisc_watchdog *wd = container_of(timer, struct qdisc_watchdog, in qdisc_watchdog() local
593 __netif_schedule(qdisc_root(wd->qdisc)); in qdisc_watchdog()
599 void qdisc_watchdog_init_clockid(struct qdisc_watchdog *wd, struct Qdisc *qdisc, in qdisc_watchdog_init_clockid() argument
602 hrtimer_init(&wd->timer, clockid, HRTIMER_MODE_ABS_PINNED); in qdisc_watchdog_init_clockid()
603 wd->timer.function = qdisc_watchdog; in qdisc_watchdog_init_clockid()
604 wd->qdisc = qdisc; in qdisc_watchdog_init_clockid()
608 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc) in qdisc_watchdog_init() argument
610 qdisc_watchdog_init_clockid(wd, qdisc, CLOCK_MONOTONIC); in qdisc_watchdog_init()
614 void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, u64 expires) in qdisc_watchdog_schedule_ns() argument
617 &qdisc_root_sleeping(wd->qdisc)->state)) in qdisc_watchdog_schedule_ns()
[all …]
/Linux-v4.19/Documentation/devicetree/bindings/arm/
Doxnas.txt13 - "wd,mbwe" (OX810SE)

12