/linux/drivers/scsi/ |
H A D | wd719x.c | 50 static inline u8 wd719x_readb(struct wd719x *wd, u8 reg) in wd719x_readb() argument 52 return ioread8(wd->base + reg); in wd719x_readb() 55 static inline u32 wd719x_readl(struct wd719x *wd, u8 reg) in wd719x_readl() argument 57 return ioread32(wd->base + reg); in wd719x_readl() 60 static inline void wd719x_writeb(struct wd719x *wd, u8 reg, u8 val) in wd719x_writeb() argument 62 iowrite8(val, wd->base + reg); in wd719x_writeb() 65 static inline void wd719x_writew(struct wd719x *wd, u8 reg, u16 val) in wd719x_writew() argument 67 iowrite16(val, wd->base + reg); in wd719x_writew() 70 static inline void wd719x_writel(struct wd719x *wd, u8 reg, u32 val) in wd719x_writel() argument 72 iowrite32(val, wd->base + reg); in wd719x_writel() [all …]
|
/linux/drivers/watchdog/ |
H A D | f71808e_wdt.c | 215 struct fintek_wdt *wd = watchdog_get_drvdata(wdd); in fintek_wdt_set_timeout() local 218 wd->timer_val = DIV_ROUND_UP(timeout, 60); in fintek_wdt_set_timeout() 219 wd->minutes_mode = true; in fintek_wdt_set_timeout() 220 timeout = wd->timer_val * 60; in fintek_wdt_set_timeout() 222 wd->timer_val = timeout; in fintek_wdt_set_timeout() 223 wd->minutes_mode = false; in fintek_wdt_set_timeout() 231 static int fintek_wdt_set_pulse_width(struct fintek_wdt *wd, unsigned int pw) in fintek_wdt_set_pulse_width() argument 235 if (wd->type == f71868) { in fintek_wdt_set_pulse_width() 242 wd->pulse_val = 0; in fintek_wdt_set_pulse_width() 244 wd->pulse_val = 1; in fintek_wdt_set_pulse_width() [all …]
|
H A D | pseries-wdt.c | 95 struct watchdog_device wd; member 178 pw->wd.parent = &pdev->dev; in pseries_wdt_probe() 179 pw->wd.info = &pseries_wdt_info; in pseries_wdt_probe() 180 pw->wd.ops = &pseries_wdt_ops; in pseries_wdt_probe() 182 pw->wd.min_timeout = DIV_ROUND_UP(msecs, MSEC_PER_SEC); in pseries_wdt_probe() 183 pw->wd.max_timeout = UINT_MAX / 1000; /* from linux/watchdog.h */ in pseries_wdt_probe() 184 pw->wd.timeout = timeout; in pseries_wdt_probe() 185 if (watchdog_init_timeout(&pw->wd, 0, NULL)) in pseries_wdt_probe() 187 watchdog_set_nowayout(&pw->wd, nowayout); in pseries_wdt_probe() 188 watchdog_stop_on_reboot(&pw->wd); in pseries_wdt_probe() [all …]
|
H A D | intel-mid_wdt.c | 41 struct watchdog_device wd; member 55 static int wdt_start(struct watchdog_device *wd) in wdt_start() argument 57 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_start() 59 int timeout = wd->timeout; in wdt_start() 81 static int wdt_ping(struct watchdog_device *wd) in wdt_ping() argument 83 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_ping() 93 static int wdt_stop(struct watchdog_device *wd) in wdt_stop() argument 95 struct mid_wdt *mid = watchdog_get_drvdata(wd); in wdt_stop() 149 wdt_dev = &mid->wd; in mid_wdt_probe()
|
/linux/sound/soc/au1x/ |
H A D | psc-i2s.c | 297 struct au1xpsc_audio_data *wd; in au1xpsc_i2s_drvprobe() local 299 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_i2s_drvprobe() 301 if (!wd) in au1xpsc_i2s_drvprobe() 304 wd->mmio = devm_platform_ioremap_resource(pdev, 0); in au1xpsc_i2s_drvprobe() 305 if (IS_ERR(wd->mmio)) in au1xpsc_i2s_drvprobe() 306 return PTR_ERR(wd->mmio); in au1xpsc_i2s_drvprobe() 311 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_i2s_drvprobe() 316 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_i2s_drvprobe() 321 sel = __raw_readl(PSC_SEL(wd)) & PSC_SEL_CLK_MASK; in au1xpsc_i2s_drvprobe() 322 __raw_writel(PSC_CTRL_DISABLE, PSC_CTRL(wd)); in au1xpsc_i2s_drvprobe() [all …]
|
H A D | psc-ac97.c | 368 struct au1xpsc_audio_data *wd; in au1xpsc_ac97_drvprobe() local 370 wd = devm_kzalloc(&pdev->dev, sizeof(struct au1xpsc_audio_data), in au1xpsc_ac97_drvprobe() 372 if (!wd) in au1xpsc_ac97_drvprobe() 375 mutex_init(&wd->lock); in au1xpsc_ac97_drvprobe() 377 wd->mmio = devm_platform_ioremap_resource(pdev, 0); in au1xpsc_ac97_drvprobe() 378 if (IS_ERR(wd->mmio)) in au1xpsc_ac97_drvprobe() 379 return PTR_ERR(wd->mmio); in au1xpsc_ac97_drvprobe() 384 wd->dmaids[SNDRV_PCM_STREAM_PLAYBACK] = dmares->start; in au1xpsc_ac97_drvprobe() 389 wd->dmaids[SNDRV_PCM_STREAM_CAPTURE] = dmares->start; in au1xpsc_ac97_drvprobe() 392 wd->cfg = PSC_AC97CFG_RT_FIFO8 | PSC_AC97CFG_TT_FIFO8 | in au1xpsc_ac97_drvprobe() [all …]
|
/linux/arch/mips/include/asm/ |
H A D | asmmacro.h | 267 .macro ld_b wd, off, base 272 ld.b $w\wd, \off(\base) 276 .macro ld_h wd, off, base 281 ld.h $w\wd, \off(\base) 285 .macro ld_w wd, off, base 290 ld.w $w\wd, \off(\base) 294 .macro ld_d wd, off, base 299 ld.d $w\wd, \off(\base) 303 .macro st_b wd, off, base 308 st.b $w\wd, \off(\base) [all …]
|
/linux/Documentation/translations/zh_CN/core-api/ |
H A D | errseq.rst | 70 struct worker_drone wd; 72 wd.wd_err = (errseq_t)0; 84 su.s_wd_err = errseq_sample(&wd.wd_err); 91 err = errseq_check_and_advance(&wd.wd_err, &su.s_wd_err); 99 errseq_set(&wd.wd_err, -EIO); 112 errseq_t since = errseq_sample(&wd.wd_err); 114 err = errseq_check(&wd.wd_err, since); 131 if (errseq_check(&wd.wd_err, READ_ONCE(su.s_wd_err)) { 134 err = errseq_check_and_advance(&wd.wd_err, &su.s_wd_err);
|
/linux/kernel/ |
H A D | usermode_driver.c | 64 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/ |
H A D | glue.c | 138 struct find_child_walk_data *wd = data; in check_one_child() local 141 if (!adev->pnp.type.bus_address || acpi_device_adr(adev) != wd->address) in check_one_child() 144 if (!wd->adev) { in check_one_child() 150 wd->adev = adev; in check_one_child() 151 return !(wd->check_sta || wd->check_children); in check_one_child() 162 if (!wd->score) { in check_one_child() 163 score = find_child_checks(wd->adev, wd->check_children); in check_one_child() 167 wd->score = score; in check_one_child() 174 score = find_child_checks(adev, wd->check_children); in check_one_child() 175 if (score > wd->score) { in check_one_child() [all …]
|
/linux/arch/mips/sgi-ip30/ |
H A D | ip30-xtalk.c | 42 struct sgi_w1_platform_data *wd; in bridge_platform_create() local 47 wd = kzalloc(sizeof(*wd), GFP_KERNEL); in bridge_platform_create() 48 if (!wd) { in bridge_platform_create() 53 snprintf(wd->dev_id, sizeof(wd->dev_id), "bridge-%012lx", in bridge_platform_create() 71 if (platform_device_add_data(pdev_wd, wd, sizeof(*wd))) { in bridge_platform_create() 80 kfree(wd); in bridge_platform_create() 133 kfree(wd); in bridge_platform_create()
|
/linux/fs/notify/inotify/ |
H A D | inotify_fsnotify.c | 42 (old->wd == new->wd) && in event_compare() 68 int len = 0, wd; in inotify_handle_inode_event() local 87 wd = READ_ONCE(i_mark->wd); in inotify_handle_inode_event() 88 if (wd == -1) in inotify_handle_inode_event() 120 event->wd = wd; in inotify_handle_inode_event() 174 fsn_mark->group, i_mark->wd); in idr_callback()
|
H A D | inotify_user.c | 220 inotify_event.wd = event->wd; in copy_event_to_user() 405 i_mark->wd = ret; in inotify_add_to_idr() 415 int wd) in inotify_idr_find_locked() argument 423 i_mark = idr_find(idr, wd); in inotify_idr_find_locked() 436 int wd) in inotify_idr_find() argument 442 i_mark = inotify_idr_find_locked(group, wd); in inotify_idr_find() 458 int wd; in inotify_remove_from_idr() local 461 wd = i_mark->wd; in inotify_remove_from_idr() 467 if (wd == -1) { in inotify_remove_from_idr() 469 __func__, i_mark, i_mark->wd, i_mark->fsn_mark.group); in inotify_remove_from_idr() [all …]
|
H A D | inotify.h | 9 int wd; member 17 int wd; member
|
/linux/arch/mips/sgi-ip27/ |
H A D | ip27-xtalk.c | 29 struct sgi_w1_platform_data *wd; in bridge_platform_create() local 37 wd = kzalloc(sizeof(*wd), GFP_KERNEL); in bridge_platform_create() 38 if (!wd) { in bridge_platform_create() 43 snprintf(wd->dev_id, sizeof(wd->dev_id), "bridge-%012lx", in bridge_platform_create() 61 if (platform_device_add_data(pdev_wd, wd, sizeof(*wd))) { in bridge_platform_create() 70 kfree(wd); in bridge_platform_create() 124 kfree(wd); in bridge_platform_create()
|
/linux/include/net/ |
H A D | pkt_sched.h | 71 void qdisc_watchdog_init_clockid(struct qdisc_watchdog *wd, struct Qdisc *qdisc, 73 void qdisc_watchdog_init(struct qdisc_watchdog *wd, struct Qdisc *qdisc); 75 void qdisc_watchdog_schedule_range_ns(struct qdisc_watchdog *wd, u64 expires, 78 static inline void qdisc_watchdog_schedule_ns(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule_ns() argument 81 return qdisc_watchdog_schedule_range_ns(wd, expires, 0ULL); in qdisc_watchdog_schedule_ns() 84 static inline void qdisc_watchdog_schedule(struct qdisc_watchdog *wd, in qdisc_watchdog_schedule() argument 87 qdisc_watchdog_schedule_ns(wd, PSCHED_TICKS2NS(expires)); in qdisc_watchdog_schedule() 90 void qdisc_watchdog_cancel(struct qdisc_watchdog *wd);
|
/linux/drivers/usb/misc/ |
H A D | usb-ljca.c | 424 struct ljca_match_ids_walk_data *wd = data; in ljca_match_device_ids() local 427 if (acpi_match_device_ids(adev, wd->ids)) in ljca_match_device_ids() 430 if (!wd->uid) in ljca_match_device_ids() 444 uid = strchr(uid, wd->uid[0]); in ljca_match_device_ids() 446 if (!uid || strcmp(uid, wd->uid)) in ljca_match_device_ids() 450 wd->adev = adev; in ljca_match_device_ids() 460 struct ljca_match_ids_walk_data wd = { 0 }; in ljca_auxdev_acpi_bind() local 475 wd.ids = ljca_gpio_hids; in ljca_auxdev_acpi_bind() 480 wd.uid = uid; in ljca_auxdev_acpi_bind() 481 wd.ids = ljca_i2c_hids; in ljca_auxdev_acpi_bind() [all …]
|
/linux/lib/raid6/ |
H A D | int.uc | 81 unative_t wd$$, wq$$, wp$$, w1$$, w2$$; 90 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; 91 wp$$ ^= wd$$; 96 wq$$ = w1$$ ^ wd$$; 110 unative_t wd$$, wq$$, wp$$, w1$$, w2$$; 120 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; 121 wp$$ ^= wd$$; 126 wq$$ = w1$$ ^ wd$$;
|
H A D | neon.uc | 63 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$$);
|
H A D | vpermxor.uc | 49 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$$);
|
H A D | altivec.uc | 77 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/ |
H A D | hid-logitech-hidpp.c | 2454 struct hidpp_ff_work_data *wd = container_of(w, struct hidpp_ff_work_data, work); in hidpp_ff_work_handler() local 2455 struct hidpp_ff_private_data *data = wd->data; in hidpp_ff_work_handler() 2461 switch (wd->effect_id) { in hidpp_ff_work_handler() 2463 wd->params[0] = data->slot_autocenter; in hidpp_ff_work_handler() 2470 wd->params[0] = hidpp_ff_find_effect(data, wd->effect_id); in hidpp_ff_work_handler() 2476 wd->command, wd->params, wd->size, &response); in hidpp_ff_work_handler() 2484 switch (wd->command) { in hidpp_ff_work_handler() 2488 if (wd->effect_id >= 0) in hidpp_ff_work_handler() 2490 data->effect_ids[slot-1] = wd->effect_id; in hidpp_ff_work_handler() 2491 else if (wd->effect_id >= HIDPP_FF_EFFECTID_AUTOCENTER) in hidpp_ff_work_handler() [all …]
|
/linux/drivers/base/power/ |
H A D | main.c | 501 #define DECLARE_DPM_WATCHDOG_ON_STACK(wd) \ argument 502 struct dpm_watchdog wd 514 struct dpm_watchdog *wd = from_timer(wd, t, timer); in dpm_watchdog_handler() local 516 dev_emerg(wd->dev, "**** DPM device timeout ****\n"); in dpm_watchdog_handler() 517 show_stack(wd->tsk, NULL, KERN_EMERG); in dpm_watchdog_handler() 519 dev_driver_string(wd->dev), dev_name(wd->dev)); in dpm_watchdog_handler() 527 static void dpm_watchdog_set(struct dpm_watchdog *wd, struct device *dev) in dpm_watchdog_set() argument 529 struct timer_list *timer = &wd->timer; in dpm_watchdog_set() 531 wd->dev = dev; in dpm_watchdog_set() 532 wd->tsk = current; in dpm_watchdog_set() [all …]
|
/linux/Documentation/core-api/ |
H A D | errseq.rst | 71 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/drivers/mfd/ |
H A D | mfd-core.c | 44 struct match_ids_walk_data *wd = data; in match_device_ids() local 46 if (!acpi_match_device_ids(adev, wd->ids)) { in match_device_ids() 47 wd->adev = adev; in match_device_ids() 77 struct match_ids_walk_data wd = { in mfd_acpi_add_device() local 83 acpi_dev_for_each_child(parent, match_device_ids, &wd); in mfd_acpi_add_device() 84 adev = wd.adev; in mfd_acpi_add_device()
|