Home
last modified time | relevance | path

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

123

/linux/drivers/scsi/
A Dwd719x.c176 dma_free_coherent(&wd->pdev->dev, wd->fw_size, wd->fw_virt, in wd719x_destroy()
183 wd->params, wd->params_phys); in wd719x_destroy()
185 free_irq(wd->pdev->irq, wd); in wd719x_destroy()
330 wd->fw_virt = dma_alloc_coherent(&wd->pdev->dev, wd->fw_size, in wd719x_chip_init()
822 wd->type = wd719x_detect_type(wd); in wd719x_board_found()
824 wd->sh = sh; in wd719x_board_found()
829 wd->params = dma_alloc_coherent(&wd->pdev->dev, in wd719x_board_found()
838 wd->hash_virt = dma_alloc_coherent(&wd->pdev->dev, in wd719x_board_found()
870 free_irq(wd->pdev->irq, wd); in wd719x_board_found()
876 wd->params, wd->params_phys); in wd719x_board_found()
[all …]
/linux/drivers/watchdog/
A Df71808e_wdt.c240 wd->pulse_val = 0; in fintek_wdt_set_pulse_width()
242 wd->pulse_val = 1; in fintek_wdt_set_pulse_width()
244 wd->pulse_val = 2; in fintek_wdt_set_pulse_width()
246 wd->pulse_val = 3; in fintek_wdt_set_pulse_width()
252 wd->pulse_mode = pw; in fintek_wdt_set_pulse_width()
278 wd->timer_val); in fintek_wdt_keepalive()
302 switch (wd->type) { in fintek_wdt_start()
376 if (wd->type == f81865 || wd->type == f81866) in fintek_wdt_start()
458 wd = devm_kzalloc(dev, sizeof(*wd), GFP_KERNEL); in fintek_wdt_probe()
459 if (!wd) in fintek_wdt_probe()
[all …]
A Dintel-mid_wdt.c37 struct watchdog_device wd; member
51 static int wdt_start(struct watchdog_device *wd) in wdt_start() argument
53 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_start()
55 int timeout = wd->timeout; in wdt_start()
77 static int wdt_ping(struct watchdog_device *wd) in wdt_ping() argument
79 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_ping()
89 static int wdt_stop(struct watchdog_device *wd) in wdt_stop() argument
91 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_stop()
145 wdt_dev = &mid->wd; in mid_wdt_probe()
/linux/sound/soc/au1x/
A Dpsc-i2s.c296 struct au1xpsc_audio_data *wd; in au1xpsc_i2s_drvprobe() local
300 if (!wd) in au1xpsc_i2s_drvprobe()
304 if (IS_ERR(wd->mmio)) in au1xpsc_i2s_drvprobe()
305 return PTR_ERR(wd->mmio); in au1xpsc_i2s_drvprobe()
324 __raw_writel(0, I2S_CFG(wd)); in au1xpsc_i2s_drvprobe()
340 platform_set_drvdata(pdev, wd); in au1xpsc_i2s_drvprobe()
350 __raw_writel(0, I2S_CFG(wd)); in au1xpsc_i2s_drvremove()
364 wd->pm[0] = __raw_readl(PSC_SEL(wd)); in au1xpsc_i2s_drvsuspend()
366 __raw_writel(0, I2S_CFG(wd)); in au1xpsc_i2s_drvsuspend()
381 __raw_writel(0, PSC_SEL(wd)); in au1xpsc_i2s_drvresume()
[all …]
A Dpsc-ac97.c367 struct au1xpsc_audio_data *wd; in au1xpsc_ac97_drvprobe() local
371 if (!wd) in au1xpsc_ac97_drvprobe()
374 mutex_init(&wd->lock); in au1xpsc_ac97_drvprobe()
377 if (IS_ERR(wd->mmio)) in au1xpsc_ac97_drvprobe()
378 return PTR_ERR(wd->mmio); in au1xpsc_ac97_drvprobe()
398 __raw_writel(0, PSC_SEL(wd)); in au1xpsc_ac97_drvprobe()
415 &wd->dai_drv, 1); in au1xpsc_ac97_drvprobe()
419 au1xpsc_ac97_workdata = wd; in au1xpsc_ac97_drvprobe()
430 __raw_writel(0, AC97_CFG(wd)); in au1xpsc_ac97_drvremove()
446 wd->pm[0] = __raw_readl(PSC_SEL(wd)); in au1xpsc_ac97_drvsuspend()
[all …]
/linux/arch/mips/include/asm/
A Dasmmacro.h266 ld.b $w\wd, \off(\base)
275 ld.h $w\wd, \off(\base)
351 .macro insert_w wd, n
356 insert.w $w\wd[\n], $1
360 .macro insert_d wd, n
365 insert.d $w\wd[\n], $1
491 .macro insert_w wd, n
500 .macro insert_d wd, n
611 insert_d \wd, 1
613 insert_w \wd, 2
[all …]
/linux/fs/hfsplus/
A Dwrapper.c111 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()
166 struct hfsplus_wd wd; in hfsplus_read_wrapper() local
204 wd.ablk_size >>= HFSPLUS_SECTOR_SHIFT; in hfsplus_read_wrapper()
205 part_start += (sector_t)wd.ablk_start + in hfsplus_read_wrapper()
206 (sector_t)wd.embed_start * wd.ablk_size; in hfsplus_read_wrapper()
[all …]
/linux/kernel/
A Dusermode_driver.c64 if (WARN_ON_ONCE(info->wd.dentry || info->wd.mnt)) in umd_load_blob()
71 info->wd.mnt = mnt; in umd_load_blob()
72 info->wd.dentry = mnt->mnt_root; in umd_load_blob()
84 if (WARN_ON_ONCE(!info->wd.mnt || in umd_unload_blob()
85 !info->wd.dentry || in umd_unload_blob()
86 info->wd.mnt->mnt_root != info->wd.dentry)) in umd_unload_blob()
89 kern_unmount(info->wd.mnt); in umd_unload_blob()
90 info->wd.mnt = NULL; in umd_unload_blob()
91 info->wd.dentry = NULL; in umd_unload_blob()
130 set_fs_pwd(current->fs, &umd_info->wd); in umd_setup()
/linux/drivers/acpi/arm64/
A Dgtdt.c64 struct acpi_gtdt_watchdog *wd = platform_timer; in is_non_secure_watchdog() local
69 return !(wd->timer_flags & ACPI_GTDT_WATCHDOG_SECURE); in is_non_secure_watchdog()
328 static int __init gtdt_import_sbsa_gwdt(struct acpi_gtdt_watchdog *wd, in gtdt_import_sbsa_gwdt() argument
339 DEFINE_RES_MEM(wd->control_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
340 DEFINE_RES_MEM(wd->refresh_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
346 wd->refresh_frame_address, wd->control_frame_address, in gtdt_import_sbsa_gwdt()
347 wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
349 if (!(wd->refresh_frame_address && wd->control_frame_address)) { in gtdt_import_sbsa_gwdt()
354 irq = map_gt_gsi(wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
369 acpi_unregister_gsi(wd->timer_interrupt); in gtdt_import_sbsa_gwdt()
/linux/arch/mips/sgi-ip30/
A Dip30-xtalk.c42 struct sgi_w1_platform_data *wd; in bridge_platform_create() local
46 wd = kzalloc(sizeof(*wd), GFP_KERNEL); in bridge_platform_create()
47 if (!wd) in bridge_platform_create()
50 snprintf(wd->dev_id, sizeof(wd->dev_id), "bridge-%012lx", in bridge_platform_create()
61 kfree(wd); in bridge_platform_create()
65 platform_device_add_data(pdev, wd, sizeof(*wd)); in bridge_platform_create()
/linux/fs/notify/inotify/
A Dinotify_user.c198 inotify_event.wd = event->wd; in copy_event_to_user()
383 i_mark->wd = ret; in inotify_add_to_idr()
393 int wd) in inotify_idr_find_locked() argument
414 int wd) in inotify_idr_find() argument
436 int wd; in inotify_remove_from_idr() local
439 wd = i_mark->wd; in inotify_remove_from_idr()
445 if (wd == -1) { in inotify_remove_from_idr()
484 idr_remove(idr, wd); in inotify_remove_from_idr()
488 i_mark->wd = -1; in inotify_remove_from_idr()
560 ret = i_mark->wd; in inotify_update_existing_watch()
[all …]
A Dinotify_fsnotify.c42 (old->wd == new->wd) && in event_compare()
113 event->wd = i_mark->wd; in inotify_handle_inode_event()
167 fsn_mark->group, i_mark->wd); in idr_callback()
A Dinotify.h9 int wd; member
17 int wd; member
/linux/arch/mips/sgi-ip27/
A Dip27-xtalk.c29 struct sgi_w1_platform_data *wd; in bridge_platform_create() local
36 wd = kzalloc(sizeof(*wd), GFP_KERNEL); in bridge_platform_create()
37 if (!wd) in bridge_platform_create()
40 snprintf(wd->dev_id, sizeof(wd->dev_id), "bridge-%012lx", in bridge_platform_create()
51 kfree(wd); in bridge_platform_create()
55 platform_device_add_data(pdev, wd, sizeof(*wd)); in bridge_platform_create()
/linux/include/net/
A Dpkt_sched.h78 void qdisc_watchdog_init_clockid(struct qdisc_watchdog *wd, struct Qdisc *qdisc,
80 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc);
82 void qdisc_watchdog_schedule_range_ns(struct qdisc_watchdog *wd, u64 expires,
85 static inline void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule_ns() argument
88 return qdisc_watchdog_schedule_range_ns(wd, expires, 0ULL); in qdisc_watchdog_schedule_ns()
91 static inline void qdisc_watchdog_schedule(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule() argument
94 qdisc_watchdog_schedule_ns(wd, PSCHED_TICKS2NS(expires)); in qdisc_watchdog_schedule()
97 void qdisc_watchdog_cancel(struct qdisc_watchdog *wd);
/linux/lib/raid6/
A 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$$;
A Dneon.uc62 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
72 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
73 wp$$ = veorq_u8(wp$$, wd$$);
79 wq$$ = veorq_u8(w1$$, wd$$);
93 register unative_t wd$$, wq$$, wp$$, w1$$, w2$$;
106 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
107 wp$$ = veorq_u8(wp$$, wd$$);
113 wq$$ = veorq_u8(w1$$, wd$$);
A 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$$);
A 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/drivers/hid/
A Dhid-logitech-hidpp.c2218 wd->params[0] = hidpp_ff_find_effect(data, wd->effect_id); in hidpp_ff_work_handler()
2224 wd->command, wd->params, wd->size, &response); in hidpp_ff_work_handler()
2253 data->gain = (wd->params[0] << 8) + wd->params[1]; in hidpp_ff_work_handler()
2256 data->range = (wd->params[0] << 8) + wd->params[1]; in hidpp_ff_work_handler()
2265 kfree(wd); in hidpp_ff_work_handler()
2270 struct hidpp_ff_work_data *wd = kzalloc(sizeof(*wd), GFP_KERNEL); in hidpp_ff_queue_work() local
2273 if (!wd) in hidpp_ff_queue_work()
2278 wd->data = data; in hidpp_ff_queue_work()
2281 wd->size = size; in hidpp_ff_queue_work()
2707 wd->flip_y ? wd->y_size - touch_report->y : in wtp_touch_event()
[all …]
/linux/drivers/base/power/
A Dmain.c503 struct dpm_watchdog wd
515 struct dpm_watchdog *wd = from_timer(wd, t, timer); in dpm_watchdog_handler() local
520 dev_driver_string(wd->dev), dev_name(wd->dev)); in dpm_watchdog_handler()
532 wd->dev = dev; in dpm_watchdog_set()
533 wd->tsk = current; in dpm_watchdog_set()
901 DECLARE_DPM_WATCHDOG_ON_STACK(wd); in device_resume()
918 dpm_watchdog_set(&wd, dev); in device_resume()
971 dpm_watchdog_clear(&wd); in device_resume()
1611 DECLARE_DPM_WATCHDOG_ON_STACK(wd); in __device_suspend()
1665 dpm_watchdog_set(&wd, dev); in __device_suspend()
[all …]
/linux/Documentation/core-api/
A 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/Documentation/devicetree/bindings/gpio/
A Dwd,mbl-gpio.txt8 - compatible: should be "wd,mbl-gpio"
24 compatible = "wd,mbl-gpio";
32 compatible = "wd,mbl-gpio";
/linux/kernel/time/
A Dtick-broadcast.c106 static void tick_oneshot_wakeup_handler(struct clock_event_device *wd) in tick_oneshot_wakeup_handler() argument
933 struct clock_event_device *dev, *wd; in tick_oneshot_wakeup_control() local
939 wd = tick_get_oneshot_wakeup_device(cpu); in tick_oneshot_wakeup_control()
940 if (!wd) in tick_oneshot_wakeup_control()
946 clockevents_switch_state(wd, CLOCK_EVT_STATE_ONESHOT); in tick_oneshot_wakeup_control()
947 clockevents_program_event(wd, dev->next_event, 1); in tick_oneshot_wakeup_control()
951 if (clockevent_get_state(wd) != CLOCK_EVT_STATE_ONESHOT) in tick_oneshot_wakeup_control()
/linux/drivers/net/ethernet/qlogic/qlcnic/
A Dqlcnic_hw.c31 u32 wd[4]; member
1304 ms->wd[0] = QLCNIC_MS_WRTDATA_LO; in qlcnic_set_ms_controls()
1306 ms->wd[1] = QLCNIC_MS_WRTDATA_HI; in qlcnic_set_ms_controls()
1308 ms->wd[2] = QLCNIC_MS_WRTDATA_ULO; in qlcnic_set_ms_controls()
1309 ms->wd[3] = QLCNIC_MS_WRTDATA_UHI; in qlcnic_set_ms_controls()
1313 ms->wd[0] = QLCNIC_MS_WRTDATA_ULO; in qlcnic_set_ms_controls()
1315 ms->wd[1] = QLCNIC_MS_WRTDATA_UHI; in qlcnic_set_ms_controls()
1317 ms->wd[2] = QLCNIC_MS_WRTDATA_LO; in qlcnic_set_ms_controls()
1318 ms->wd[3] = QLCNIC_MS_WRTDATA_HI; in qlcnic_set_ms_controls()
1375 qlcnic_ind_wr(adapter, ms.wd[2], data & 0xffffffff); in qlcnic_pci_mem_write_2M()
[all …]

Completed in 867 milliseconds

123