Home
last modified time | relevance | path

Searched full:current (Results 1 – 25 of 4387) sorted by relevance

12345678910>>...176

/linux/kernel/
H A Ddelayacct.c126 current->delays->blkio_start = local_clock(); in __delayacct_blkio_start()
130 * We cannot rely on the `current` macro, as we haven't yet switched back to
210 current->delays->freepages_start = local_clock(); in __delayacct_freepages_start()
215 delayacct_end(&current->delays->lock, in __delayacct_freepages_end()
216 &current->delays->freepages_start, in __delayacct_freepages_end()
217 &current->delays->freepages_delay, in __delayacct_freepages_end()
218 &current->delays->freepages_count, in __delayacct_freepages_end()
219 &current->delays->freepages_delay_max, in __delayacct_freepages_end()
220 &current->delays->freepages_delay_min); in __delayacct_freepages_end()
225 *in_thrashing = !!current->in_thrashing; in __delayacct_thrashing_start()
[all …]
/linux/arch/sparc/kernel/
H A Dsigutil_32.c19 if (test_tsk_thread_flag(current, TIF_USEDFPU)) { in save_fpu_state()
21 fpsave(&current->thread.float_regs[0], &current->thread.fsr, in save_fpu_state()
22 &current->thread.fpqueue[0], &current->thread.fpqdepth); in save_fpu_state()
24 clear_tsk_thread_flag(current, TIF_USEDFPU); in save_fpu_state()
27 if (current == last_task_used_math) { in save_fpu_state()
29 fpsave(&current->thread.float_regs[0], &current->thread.fsr, in save_fpu_state()
30 &current->thread.fpqueue[0], &current->thread.fpqdepth); in save_fpu_state()
36 &current->thread.float_regs[0], in save_fpu_state()
38 err |= __put_user(current->thread.fsr, &fpu->si_fsr); in save_fpu_state()
39 err |= __put_user(current->thread.fpqdepth, &fpu->si_fpqdepth); in save_fpu_state()
[all …]
/linux/Documentation/hwmon/
H A Dmax16601.rst83 curr1_input VCORE input current, derived from duty cycle
84 and output current.
85 curr1_max Maximum input current.
86 curr1_max_alarm Current high alarm.
89 curr[P+2]_input VCORE phase P input current.
92 curr[N+2]_input VCORE input current, derived from sensor
97 curr[N+3]_input VSA input current.
100 curr[N+4]_input VCORE output current.
101 curr[N+4]_crit Critical output current.
102 curr[N+4]_crit_alarm Output current critical alarm.
[all …]
H A Dina3221.rst21 The Texas Instruments INA3221 monitors voltage, current, and power on the high
23 and supply voltage, with programmable conversion times and averaging, current
33 curr[123]_input Current(mA) measurement channels
35 curr[123]_crit Critical alert current(mA) setting, activates the
36 corresponding alarm when the respective current
38 curr[123]_crit_alarm Critical alert current limit exceeded
39 curr[123]_max Warning alert current(mA) setting, activates the
40 corresponding alarm when the respective current
42 curr[123]_max_alarm Warning alert current limit exceeded
46 curr4_input Sum of current(mA) measurement channels,
[all …]
H A Dmax16065.rst55 accurately monitor (+/-2.5%) one current channel using a dedicated high-side
56 current-sense amplifier. The MAX16065 manages up to twelve system voltages
67 one current channel using a dedicated high-side current-sense amplifier. The
74 MAX16070, and MAX16071 also support supply current monitoring.
99 in12_input Voltage on CSP (Current Sense Positive) pin.
100 Only if the chip supports current sensing and if
101 current sensing is enabled.
120 curr1_input Current sense input; only if the chip supports current
121 sensing and if current sensing is enabled.
122 Displayed current assumes 0.001 Ohm current sense
[all …]
H A Dacbel-fsg032.rst29 curr1_crit Critical maximum current.
30 curr1_crit_alarm Input current critical alarm.
31 curr1_input Measured output current.
33 curr1_max Maximum input current.
34 curr1_max_alarm Maximum input current high alarm.
35 curr1_rated_max Maximum rated input current.
36 curr2_crit Critical maximum current.
37 curr2_crit_alarm Output current critical alarm.
38 curr2_input Measured output current.
40 curr2_max Maximum output current.
[all …]
/linux/include/linux/platform_data/
H A Dad7793.h54 * enum ad7793_current_source_direction - AD7793 excitation current direction
55 * @AD7793_IEXEC1_IOUT1_IEXEC2_IOUT2: Current source IEXC1 connected to pin
56 * IOUT1, current source IEXC2 connected to pin IOUT2.
57 * @AD7793_IEXEC1_IOUT2_IEXEC2_IOUT1: Current source IEXC2 connected to pin
58 * IOUT1, current source IEXC1 connected to pin IOUT2.
59 * @AD7793_IEXEC1_IEXEC2_IOUT1: Both current sources connected to pin IOUT1.
60 * Only valid when the current sources are set to 10 uA or 210 uA.
61 * @AD7793_IEXEC1_IEXEC2_IOUT2: Both current sources connected to Pin IOUT2.
62 * Only valid when the current ources are set to 10 uA or 210 uA.
72 * enum ad7793_excitation_current - AD7793 excitation current selection
[all …]
/linux/arch/powerpc/kernel/
H A Dsignal_32.c243 * Save the current user registers on the user stack.
250 flush_fp_to_thread(current); in prepare_save_user_regs()
252 if (current->thread.used_vr) in prepare_save_user_regs()
253 flush_altivec_to_thread(current); in prepare_save_user_regs()
255 current->thread.vrsave = mfspr(SPRN_VRSAVE); in prepare_save_user_regs()
258 if (current->thread.used_vsr && ctx_has_vsx_region) in prepare_save_user_regs()
259 flush_vsx_to_thread(current); in prepare_save_user_regs()
262 if (current->thread.used_spe) in prepare_save_user_regs()
263 flush_spe_to_thread(current); in prepare_save_user_regs()
278 if (current->thread.used_vr) { in __unsafe_save_user_regs()
[all …]
H A Dprocess.c86 * If we are saving the current thread's registers, and the in check_if_tm_restore_required()
91 if (tsk == current && tsk->thread.regs && in check_if_tm_restore_required()
191 * This should only ever be called for current or in flush_fp_to_thread()
197 BUG_ON(tsk != current); in flush_fp_to_thread()
213 if (current->thread.regs && (current->thread.regs->msr & MSR_FP)) { in enable_kernel_fp()
214 check_if_tm_restore_required(current); in enable_kernel_fp()
223 MSR_TM_ACTIVE(current->thread.regs->msr)) in enable_kernel_fp()
225 __giveup_fpu(current); in enable_kernel_fp()
264 if (current->thread.regs && (current->thread.regs->msr & MSR_VEC)) { in enable_kernel_altivec()
265 check_if_tm_restore_required(current); in enable_kernel_altivec()
[all …]
/linux/drivers/tty/
H A Dtty_jobctrl.c18 return (sigismember(&current->blocked, sig) || in is_ignored()
19 current->sighand->action[sig-1].sa.sa_handler == SIG_IGN); in is_ignored()
39 if (current->signal->tty != tty) in __tty_check_change()
43 pgrp = task_pgrp(current); in __tty_check_change()
109 tty->ctrl.pgrp = get_pid(task_pgrp(current)); in __proc_set_tty()
110 tty->ctrl.session = get_pid(task_session(current)); in __proc_set_tty()
112 if (current->signal->tty) { in __proc_set_tty()
113 tty_debug(tty, "current tty %s not NULL!!\n", in __proc_set_tty()
114 current->signal->tty->name); in __proc_set_tty()
115 tty_kref_put(current->signal->tty); in __proc_set_tty()
[all …]
/linux/Documentation/devicetree/bindings/net/
H A Dqcom,qca807x.yaml80 With this enabled and qcom,dac-full-bias-current
81 and qcom,dac-disable-bias-current-tweak disabled,
82 bias current is half.
85 qcom,dac-full-bias-current:
87 Set Analog MDI driver bias current to FULL.
89 With this not defined, bias current is set to DSP.
90 (bias current is adjusted based on cable length)
92 Actual bias current might be different with
93 qcom,dac-disable-bias-current-tweak disabled.
96 qcom,dac-disable-bias-current-tweak:
[all …]
/linux/Documentation/devicetree/bindings/power/supply/
H A Dbq25890.yaml38 ti,charge-current:
40 description: maximum charging current (in uA)
42 ti,termination-current:
45 charge will be terminated when current in constant-voltage phase
48 ti,precharge-current:
50 description: maximum charge current during precharge phase (in uA)
62 ti,boost-max-current:
64 description: maximum allowed current draw in boost mode (in uA)
72 ILIM resistor will be used and the input current will be the lower
79 temperature above which the charge current is lowered, to avoid overheating
[all …]
H A Drohm,bd99954.yaml29 # Curve (1) represents charging current.
33 # a) Trickle-charge with constant current (8).
34 # b) pre-charge with constant current (6)
36 # First a constant current (5) phase (CC)
38 # target level - until charging current has dropped to termination
70 # - trickle-charge-current-microamp:
71 # Current used at trickle-charge phase (8 in above chart)
75 # - precharge-current-microamp:
76 # Current used at pre-charge phase (6 in above chart)
80 # - constant-charge-current-max-microamp
[all …]
H A Dsummit,smb347-charger.yaml53 summit,mains-current-limit-microamp:
54 description: Maximum input current from AC/DC input (in uA)
56 summit,usb-current-limit-microamp:
57 description: Maximum input current from USB input (in uA)
59 summit,charge-current-compensation-microamp:
60 description: Charge current compensation (in uA)
71 - 1 # SMB3XX_SOFT_TEMP_COMPENSATE_CURRENT Current compensation
105 summit,mains-current-limit-microamp:
109 summit,usb-current-limit-microamp:
113 summit,charge-current-compensation-microamp:
[all …]
H A Dbq24257.yaml33 ti,charge-current:
35 description: maximum charging current in uA
37 ti,termination-current:
40 charge will be terminated when current in constant-voltage phase
52 ti,current-limit:
55 The maximum current to be drawn from the charger's input (in uA).
56 If this property is not specified, the input limit current is set
78 - ti,charge-current
79 - ti,termination-current
100 ti,charge-current = <1000000>;
[all …]
H A Dbq2415x.yaml34 ti,current-limit:
36 description: initial maximum current charger can pull from power supply in mA.
48 ti,charge-current:
50 description: maximum charging current in mA.
52 ti,termination-current:
55 charge will be terminated when current in constant-voltage phase drops
69 - ti,current-limit
72 - ti,charge-current
73 - ti,termination-current
88 ti,current-limit = <100>;
[all …]
/linux/tools/testing/selftests/cgroup/
H A Dtest_hugetlb_memcg.c99 long old_current, expected_current, current; in hugetlb_test_program()
102 old_current = cg_read_long(test_group, "memory.current"); in hugetlb_test_program()
104 current = cg_read_long(test_group, "memory.current"); in hugetlb_test_program()
105 if (current - old_current >= MB(2)) { in hugetlb_test_program()
108 ksft_print_msg("before: %ld, after: %ld\n", old_current, current); in hugetlb_test_program()
117 current = cg_read_long(test_group, "memory.current"); in hugetlb_test_program()
118 if (current - old_current >= MB(2)) { in hugetlb_test_program()
120 ksft_print_msg("before: %ld, after: %ld\n", old_current, current); in hugetlb_test_program()
97 long old_current, expected_current, current; hugetlb_test_program() local
[all...]
/linux/arch/riscv/kernel/
H A Dkernel_mode_vector.c23 WRITE_ONCE(current->thread.riscv_v_flags, flags); in riscv_v_flags_set()
86 return &current->thread.riscv_v_flags; in riscv_v_flags_ptr()
116 if (riscv_v_ctx_get_depth() != 0 || !riscv_preempt_v_started(current)) in riscv_v_stop_kernel_context()
119 riscv_preempt_v_clear_dirty(current); in riscv_v_stop_kernel_context()
128 kvstate = &current->thread.kernel_vstate; in riscv_v_start_kernel_context()
132 if (riscv_preempt_v_started(current)) { in riscv_v_start_kernel_context()
136 if (riscv_preempt_v_dirty(current)) { in riscv_v_start_kernel_context()
138 riscv_preempt_v_clear_dirty(current); in riscv_v_start_kernel_context()
140 riscv_preempt_v_set_restore(current); in riscv_v_start_kernel_context()
146 if (__riscv_v_vstate_check(task_pt_regs(current)->status, DIRTY)) { in riscv_v_start_kernel_context()
[all …]
/linux/Documentation/devicetree/bindings/iio/addac/
H A Dadi,ad74115.yaml62 2 - Current output
64 4 - Current input, externally-powered
65 5 - Current input, loop-powered
70 10 - Current output with HART
71 11 - Current input, externally-powered, with HART
72 12 - Current input, loop-powered, with HART
146 description: Sink current in digital input mode.
192 adi,dac-current-limit-low:
195 When not present, the DAC short-circuit current limit is 32mA in
210 adi,rtd-excitation-current-microamp:
[all …]
/linux/kernel/events/
H A Dhw_breakpoint_test.c127 TEST_EXPECT_NOSPC(register_test_bp(-1, current, idx)); in test_one_cpu()
150 fill_bp_slots(test, &idx, -1, current, 0); in test_one_task_on_all_cpus()
151 TEST_EXPECT_NOSPC(register_test_bp(-1, current, idx)); in test_one_task_on_all_cpus()
152 TEST_EXPECT_NOSPC(register_test_bp(get_test_cpu(0), current, idx)); in test_one_task_on_all_cpus()
164 fill_bp_slots(test, &idx, -1, current, 0); in test_two_tasks_on_all_cpus()
167 TEST_EXPECT_NOSPC(register_test_bp(-1, current, idx)); in test_two_tasks_on_all_cpus()
169 TEST_EXPECT_NOSPC(register_test_bp(get_test_cpu(0), current, idx)); in test_two_tasks_on_all_cpus()
181 fill_bp_slots(test, &idx, get_test_cpu(0), current, 0); in test_one_task_on_one_cpu()
182 TEST_EXPECT_NOSPC(register_test_bp(-1, current, idx)); in test_one_task_on_one_cpu()
183 TEST_EXPECT_NOSPC(register_test_bp(get_test_cpu(0), current, idx)); in test_one_task_on_one_cpu()
[all …]
/linux/Documentation/power/regulator/
H A Doverview.rst2 Linux voltage and current regulator framework
9 voltage and current regulators.
13 regulators (where voltage output is controllable) and current sinks (where
14 current limit is controllable).
29 some can control their output voltage and or current.
44 current limit. It only needs to enable or disable its
49 current limit to meet operation demands.
101 - regulator current output limit is 20mA @ 5V but is
110 - Domain-3 current limit is 0mA -> 20mA.
113 dynamically setting voltage or current limit levels.
[all …]
/linux/Documentation/devicetree/bindings/phy/
H A Dphy-stm32-usbphyc.yaml94 st,current-boost-microamp:
95 description: Current boosting in uA
126 st,trim-hs-current:
128 Controls HS driver current trimming for choke compensation
129 - <0> = 18.87 mA target current / nominal + 0%
130 - <1> = 19.165 mA target current / nominal + 1.56%
131 - <2> = 19.46 mA target current / nominal + 3.12%
132 - <3> = 19.755 mA target current / nominal + 4.68%
133 - <4> = 20.05 mA target current / nominal + 6.24%
134 - <5> = 20.345 mA target current / nominal + 7.8%
[all …]
/linux/scripts/gdb/linux/
H A Dlists.py81 gdb.write('prev.next != current: '
82 'current@{current_addr}={current} '
85 current=c,
92 'current@{current_addr}={current}\n'.format(
94 current=c
99 gdb.write('next.prev != current: '
100 'current@{current_addr}={current} '
103 current=c,
110 'current@{current_addr}={current}\n'.format(
112 current=c
/linux/scripts/dtc/
H A Dsrcpos.h28 * current directory (the directory of the last source file read) and after
68 #define YYLLOC_DEFAULT(Current, Rhs, N) \ argument
71 (Current).first_line = YYRHSLOC(Rhs, 1).first_line; \
72 (Current).first_column = YYRHSLOC(Rhs, 1).first_column; \
73 (Current).last_line = YYRHSLOC(Rhs, N).last_line; \
74 (Current).last_column = YYRHSLOC (Rhs, N).last_column; \
75 (Current).file = YYRHSLOC(Rhs, N).file; \
77 (Current).first_line = (Current).last_line = \
79 (Current)
[all...]
/linux/rust/kernel/
H A Dtask.rs36 macro_rules! current {
40 // leave current task context:
42 // * To return to userspace, the caller must leave the current scope.
48 unsafe { &*$crate::task::Task::current() }
63 /// The following is an example of getting the PID of the current thread with zero additional cost
67 /// let pid = current!().pid();
70 /// Getting the PID of the current process, also zero additional cost:
73 /// let pid = current!().group_leader().pid();
76 /// Getting the current task and storing it in some struct. The reference count is automatically
90 /// creator: ARef::from(&**current!()),
35 macro_rules! current { global() macro
177 pub unsafe fn current() -> impl Deref<Target = CurrentTask> { current() method
[all...]

12345678910>>...176