Home
last modified time | relevance | path

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

12345678910>>...165

/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/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 …]
H A Drichtek,rt9455.yaml25 richtek,output-charge-current:
27 description: output current from the charger to the battery, in uA.
32 percent of the output charge current. When the current in constant-voltage phase drops
47 input voltage level in uV, used to decrease voltage level when the over current of the
49 current provided by the power source. Defaults to 4500000 uV (4.5V).
51 richtek,avg-input-current-regulation:
54 input current value in uA drained by the charger from the power source.
61 - richtek,output-charge-current
82 richtek,output-charge-current = <500000>;
88 richtek,avg-input-current-regulation = <500000>;
/linux/tools/testing/selftests/cgroup/
H A Dtest_hugetlb_memcg.c99 long old_current, expected_current, current; in hugetlb_test_program() local
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()
123 old_current = current; in hugetlb_test_program()
128 current = cg_read_long(test_group, "memory.current"); in hugetlb_test_program()
[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/hwmon/
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 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 …]
H A Dlochnagar.rst12 Lochnagar 2 features built-in Current Monitor circuitry that allows for the
13 measurement of both voltage and current on up to eight of the supply voltage
14 rails provided to the minicards. The Current Monitor does not require any
17 The current and voltage measurements are obtained through the standard register
28 curr1_input Measured current for DBVDD1 (milliAmps)
35 curr2_input Measured current for 1V8 DSP (milliAmps)
42 curr3_input Measured current for 1V8 CDC (milliAmps)
49 curr4_input Measured current for VDDCORE DSP (milliAmps)
56 curr5_input Measured current for AVDD 1V8 (milliAmps)
61 curr6_input Measured current for SYSVDD (milliAmps)
[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/rust/kernel/
H A Drbtree.rs249 let current = unsafe { bindings::rb_first(root) }; in cursor_front_mut() localVariable
250 NonNull::new(current).map(|current| { in cursor_front_mut()
252 // - `current` is a valid node in the [`RBTree`] pointed to by `self`. in cursor_front_mut()
254 current, in cursor_front_mut()
264 let current = unsafe { bindings::rb_first(root) }; in cursor_front() localVariable
265 NonNull::new(current).map(|current| { in cursor_front()
267 // - `current` is a valid node in the [`RBTree`] pointed to by `self`. in cursor_front()
269 current, in cursor_front()
279 let current = unsafe { bindings::rb_last(root) }; in cursor_back_mut() localVariable
280 NonNull::new(current).map(|current| { in cursor_back_mut()
[all …]
/linux/Documentation/admin-guide/cgroup-v1/
H A Dpids.rst21 number of processes currently in the cgroup is given by pids.current.
24 to have pids.current > pids.max. This can be done by either setting the limit to
25 be smaller than pids.current, or attaching enough processes to the cgroup such
26 that pids.current > pids.max. However, it is not possible to violate a cgroup
34 pids.current tracks all child cgroup hierarchies, so parent/pids.current is a
35 superset of parent/child/pids.current.
55 # cat /sys/fs/cgroup/pids/parent/pids.current
62 # cat /sys/fs/cgroup/pids/parent/pids.current
73 # cat /sys/fs/cgroup/pids/parent/pids.current
75 # cat /sys/fs/cgroup/pids/parent/child/pids.current
[all …]

12345678910>>...165