Home
last modified time | relevance | path

Searched full:wd (Results 1 – 25 of 113) sorted by relevance

12345

/linux/drivers/watchdog/
H A Df71808e_wdt.c215 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 Dpseries-wdt.c95 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 Dintel-mid_wdt.c41 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()
H A Dmei_wdt.c42 * @MEI_WDT_PROBE: wd in probing stage
43 * @MEI_WDT_IDLE: wd is idle and not opened
44 * @MEI_WDT_START: wd was opened, start was called
45 * @MEI_WDT_RUNNING: wd is expecting keep alive pings
46 * @MEI_WDT_STOPPING: wd is stopping and will move to IDLE
47 * @MEI_WDT_NOT_REQUIRED: wd device is not required
159 * mei_wdt_ping - send wd start/ping command
187 * mei_wdt_stop - send wd stop command
214 * mei_wdt_ops_start - wd start command from the watchdog core.
230 * mei_wdt_ops_stop - wd stop command from the watchdog core.
[all …]
H A Dmachzwd.c13 * We have two timers (wd#1, wd#2) driven by a 32 KHz clock with the
15 * wd#1 - 2 seconds;
16 * wd#2 - 7.2 ms;
17 * After the expiration of wd#1, it can generate a NMI, SCI, SMI, or
18 * a system RESET and it starts wd#2 that unconditionally will RESET
134 /* number of ticks on WD#1 (driven by a 32KHz clock, 2s) */
164 /* WD#? counter functions */
/linux/arch/mips/include/asm/
H A Dasmmacro.h267 .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/fs/befs/
H A DChangeLog23 interface into their own file called linuxvfs.c. [WD]
27 * Did the string comparison really right this time (btree.c) [WD]
30 a pointer value. (btree.c) [WD]
35 a workaround for this problem (compatibility.h) [WD]
41 * Made a debian package of the source for use with kernel-package. [WD]
48 0.61. (datastream.c) [WD]
56 (btree.c) [WD]
59 they work. I had forgotten all about them. (inode.c, symlink.c) [WD]
61 * Documentation improvements in source. [WD]
71 * Fixed makefile for module install [WD]
[all …]
/linux/drivers/acpi/
H A Dglue.c138 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/Documentation/translations/zh_CN/core-api/
H A Derrseq.rst70 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/fs/notify/inotify/
H A Dinotify_fsnotify.c42 (old->wd == new->wd) && in event_compare()
68 int len = 0, wd; in inotify_handle_inode_event() local
85 * invalid wd. in inotify_handle_inode_event()
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()
173 printk(KERN_WARNING "fsn_mark->group=%p wd=%d\n", in idr_callback()
174 fsn_mark->group, i_mark->wd); in idr_callback()
/linux/arch/mips/sgi-ip27/
H A Dip27-xtalk.c29 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/drivers/acpi/arm64/
H A Dgtdt.c70 struct acpi_gtdt_watchdog *wd = platform_timer; in is_non_secure_watchdog() local
75 return !(wd->timer_flags & ACPI_GTDT_WATCHDOG_SECURE); in is_non_secure_watchdog()
343 static int __init gtdt_import_sbsa_gwdt(struct acpi_gtdt_watchdog *wd, in gtdt_import_sbsa_gwdt() argument
354 DEFINE_RES_MEM(wd->control_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
355 DEFINE_RES_MEM(wd->refresh_frame_address, SZ_4K), in gtdt_import_sbsa_gwdt()
361 wd->refresh_frame_address, wd->control_frame_address, in gtdt_import_sbsa_gwdt()
362 wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
364 if (!(wd->refresh_frame_address && wd->control_frame_address)) { in gtdt_import_sbsa_gwdt()
369 irq = map_gt_gsi(wd->timer_interrupt, wd->timer_flags); in gtdt_import_sbsa_gwdt()
384 acpi_unregister_gsi(wd->timer_interrupt); in gtdt_import_sbsa_gwdt()
/linux/lib/raid6/
H A Dint.uc81 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 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$$);
H A Dloongarch_simd.c48 * $vr8, $vr9, $vr10, $vr11: wd in raid6_lsx_gen_syndrome()
63 /* wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; */ in raid6_lsx_gen_syndrome()
68 /* wp$$ ^= wd$$; */ in raid6_lsx_gen_syndrome()
93 /* wq$$ = w1$$ ^ wd$$; */ in raid6_lsx_gen_syndrome()
130 * $vr8, $vr9, $vr10, $vr11: wd in raid6_lsx_xor_syndrome()
146 /* wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; */ in raid6_lsx_xor_syndrome()
151 /* wp$$ ^= wd$$; */ in raid6_lsx_xor_syndrome()
176 /* wq$$ = w1$$ ^ wd$$; */ in raid6_lsx_xor_syndrome()
279 * $xr4, $xr5: wd in raid6_lasx_gen_syndrome()
290 /* wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; */ in raid6_lasx_gen_syndrome()
[all …]
H 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$$);
H A Drvv.c59 * wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; in raid6_rvv1_gen_syndrome_real()
60 * wq$$ = w1$$ ^ wd$$; in raid6_rvv1_gen_syndrome_real()
61 * wp$$ ^= wd$$; in raid6_rvv1_gen_syndrome_real()
133 * wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; in raid6_rvv1_xor_syndrome_real()
134 * wq$$ = w1$$ ^ wd$$; in raid6_rvv1_xor_syndrome_real()
135 * wp$$ ^= wd$$; in raid6_rvv1_xor_syndrome_real()
236 * wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; in raid6_rvv2_gen_syndrome_real()
237 * wq$$ = w1$$ ^ wd$$; in raid6_rvv2_gen_syndrome_real()
238 * wp$$ ^= wd$$; in raid6_rvv2_gen_syndrome_real()
329 * wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE]; in raid6_rvv2_xor_syndrome_real()
[all …]
H 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/Documentation/core-api/
H 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/tools/testing/selftests/ftrace/test.d/ftrace/
H A Dfgraph-multi.tc12 WD=`pwd`
15 cd $WD
82 cd $WD
85 cd $WD
95 cd $WD
/linux/include/net/
H A Dpkt_sched.h71 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 Dusb-ljca.c424 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/drivers/base/power/
H A Dmain.c515 #define DECLARE_DPM_WATCHDOG_ON_STACK(wd) \ argument
516 struct dpm_watchdog wd
528 struct dpm_watchdog *wd = timer_container_of(wd, t, timer); in dpm_watchdog_handler() local
529 struct timer_list *timer = &wd->timer; in dpm_watchdog_handler()
532 if (wd->fatal) { in dpm_watchdog_handler()
533 dev_emerg(wd->dev, "**** DPM device timeout ****\n"); in dpm_watchdog_handler()
534 show_stack(wd->tsk, NULL, KERN_EMERG); in dpm_watchdog_handler()
536 dev_driver_string(wd->dev), dev_name(wd->dev)); in dpm_watchdog_handler()
540 dev_warn(wd->dev, "**** DPM device timeout after %u seconds; %u seconds until panic ****\n", in dpm_watchdog_handler()
542 show_stack(wd->tsk, NULL, KERN_WARNING); in dpm_watchdog_handler()
[all …]
/linux/drivers/hid/
H A Dhid-logitech-hidpp.c2456 struct hidpp_ff_work_data *wd = container_of(w, struct hidpp_ff_work_data, work); in hidpp_ff_work_handler() local
2457 struct hidpp_ff_private_data *data = wd->data; in hidpp_ff_work_handler()
2463 switch (wd->effect_id) { in hidpp_ff_work_handler()
2465 wd->params[0] = data->slot_autocenter; in hidpp_ff_work_handler()
2472 wd->params[0] = hidpp_ff_find_effect(data, wd->effect_id); in hidpp_ff_work_handler()
2478 wd->command, wd->params, wd->size, &response); in hidpp_ff_work_handler()
2486 switch (wd->command) { in hidpp_ff_work_handler()
2490 if (wd->effect_id >= 0) in hidpp_ff_work_handler()
2492 data->effect_ids[slot-1] = wd->effect_id; in hidpp_ff_work_handler()
2493 else if (wd->effect_id >= HIDPP_FF_EFFECTID_AUTOCENTER) in hidpp_ff_work_handler()
[all …]
/linux/drivers/cxl/core/
H A Dras.c110 struct cxl_cper_prot_err_work_data wd; in cxl_cper_prot_err_work_fn() local
112 while (cxl_cper_prot_err_kfifo_get(&wd)) in cxl_cper_prot_err_work_fn()
113 cxl_cper_handle_prot_err(&wd); in cxl_cper_prot_err_work_fn()

12345