Home
last modified time | relevance | path

Searched refs:current (Results 1 – 25 of 2770) sorted by relevance

12345678910>>...111

/linux/kernel/
H A Ddelayacct.c131 current->delays->blkio_start = local_clock();
135 * We cannot rely on the `current` macro, as we haven't yet switched back to in __delayacct_blkio_end()
218 current->delays->freepages_start = local_clock(); in __delayacct_freepages_end()
223 delayacct_end(&current->delays->lock, in __delayacct_thrashing_start()
224 &current->delays->freepages_start, in __delayacct_thrashing_start()
225 &current->delays->freepages_delay, in __delayacct_thrashing_start()
226 &current->delays->freepages_count, in __delayacct_thrashing_start()
227 &current->delays->freepages_delay_max, in __delayacct_thrashing_start()
228 &current->delays->freepages_delay_min, in __delayacct_thrashing_start()
229 &current in __delayacct_thrashing_start()
[all...]
H A Dacct.c220 struct pid_namespace *ns = task_active_pid_ns(current); in acct_on()
306 pin_kill(task_active_pid_ns(current)->bacct); in SYSCALL_DEFINE1()
432 struct pacct_struct *pacct = &current->signal->pacct; in fill_ac()
458 strscpy(ac->ac_comm, current->comm, sizeof(ac->ac_comm)); in fill_ac()
462 run_time -= current->group_leader->start_time; in fill_ac()
487 spin_lock_irq(&current->sighand->siglock); in fill_ac()
488 tty = current->signal->tty; /* Safe as we hold the siglock */ in fill_ac()
497 spin_unlock_irq(&current->sighand->siglock); in fill_ac()
510 ac->ac_pid = task_tgid_nr_ns(current, ns); in fill_ac()
512 ac->ac_ppid = task_tgid_nr_ns(rcu_dereference(current->real_parent), ns); in fill_ac()
[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 …]
H A Dtraps_32.c63 printk("%s(%d): %s [#%d]\n", current->comm, task_pid_nr(current), str, ++die_counter); in die_if_kernel()
118 send_sig_fault(SIGILL, ILL_ILLOPC, (void __user *)pc, current); in do_illegal_instruction()
126 send_sig_fault(SIGILL, ILL_PRVOPC, (void __user *)pc, current); in do_priv_instruction()
147 current); in do_memaccess_unaligned()
167 if(last_task_used_math == current) in do_fpd_trap()
175 last_task_used_math = current; in do_fpd_trap()
177 fpload(&current->thread.float_regs[0], &current->thread.fsr); in do_fpd_trap()
188 fpload(&current->thread.float_regs[0], &current->thread.fsr); in do_fpd_trap()
209 struct task_struct *fpt = current;
256 fpload(&current->thread.float_regs[0], &current->thread.fsr);
[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()
114 current->signal->tty->name); in __proc_set_tty()
115 tty_kref_put(current->signal->tty); in __proc_set_tty()
117 put_pid(current->signal->tty_old_pgrp); in __proc_set_tty()
[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/arch/powerpc/kernel/
H A Dsignal_32.c250 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()
279 unsafe_copy_to_user(&frame->mc_vregs, &current->thread.vr_state, in __unsafe_save_user_regs()
[all …]
H A Duprobes.c66 struct arch_uprobe_task *autask = &current->utask->autask; in arch_uprobe_pre_xol()
68 autask->saved_trap_nr = current->thread.trap_nr; in arch_uprobe_pre_xol()
69 current->thread.trap_nr = UPROBE_TRAP_NR; in arch_uprobe_pre_xol()
70 regs_set_return_ip(regs, current->utask->xol_vaddr); in arch_uprobe_pre_xol()
72 user_enable_single_step(current); in arch_uprobe_pre_xol()
114 struct uprobe_task *utask = current->utask; in arch_uprobe_post_xol()
116 WARN_ON_ONCE(current->thread.trap_nr != UPROBE_TRAP_NR); in arch_uprobe_post_xol()
118 current->thread.trap_nr = utask->autask.saved_trap_nr; in arch_uprobe_post_xol()
129 user_disable_single_step(current); in arch_uprobe_post_xol()
170 struct uprobe_task *utask = current->utask; in arch_uprobe_abort_xol()
[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/arch/s390/kernel/
H A Dguarded_storage.c26 if (!current->thread.gs_cb) { in gs_enable()
34 current->thread.gs_cb = gs_cb; in gs_enable()
42 if (current->thread.gs_cb) { in gs_disable()
44 kfree(current->thread.gs_cb); in gs_disable()
45 current->thread.gs_cb = NULL; in gs_disable()
56 gs_cb = current->thread.gs_bc_cb; in gs_set_bc_cb()
61 current->thread.gs_bc_cb = gs_cb; in gs_set_bc_cb()
72 gs_cb = current->thread.gs_bc_cb; in gs_clear_bc_cb()
73 current->thread.gs_bc_cb = NULL; in gs_clear_bc_cb()
84 gs_cb = current->thread.gs_bc_cb; in gs_load_bc_cb()
[all …]
/linux/tools/testing/selftests/cgroup/
H A Dtest_hugetlb_memcg.c99 long old_current, expected_current, current; in hugetlb_test_program() local
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()
129 if (!values_close(expected_current, current, 5)) { in hugetlb_test_program()
[all …]
/linux/arch/m68k/mm/
H A Dfault.c29 signo = current->thread.signo; in send_fault_sig()
30 si_code = current->thread.code; in send_fault_sig()
31 addr = (void __user *)current->thread.faddr; in send_fault_sig()
73 struct mm_struct *mm = current->mm; in do_page_fault()
191 current->thread.signo = SIGBUS; in do_page_fault()
192 current->thread.faddr = address; in do_page_fault()
196 current->thread.signo = SIGBUS; in do_page_fault()
197 current->thread.code = BUS_ADRERR; in do_page_fault()
198 current->thread.faddr = address; in do_page_fault()
204 current->thread.signo = SIGSEGV; in do_page_fault()
[all …]
/linux/arch/arm64/kernel/
H A Dfpsimd.c369 switch (current->thread.fp_type) { in task_fpsimd_load()
375 if (!thread_sm_enabled(&current->thread)) in task_fpsimd_load()
379 sve_set_vq(sve_vq_from_vl(task_get_sve_vl(current)) - 1); in task_fpsimd_load()
401 unsigned long sme_vl = task_get_sme_vl(current); in task_fpsimd_load()
407 write_sysreg_s(current->thread.svcr, SYS_SVCR); in task_fpsimd_load()
409 if (thread_za_enabled(&current->thread)) in task_fpsimd_load()
410 sme_load_state(current->thread.sme_state, in task_fpsimd_load()
413 if (thread_sm_enabled(&current->thread)) in task_fpsimd_load()
418 write_sysreg_s(current->thread.uw.fpmr, SYS_FPMR); in task_fpsimd_load()
421 WARN_ON_ONCE(current->thread.fp_type != FP_STATE_SVE); in task_fpsimd_load()
[all …]
H A Dsignal.c254 &current->thread.uw.fpsimd_state; in preserve_fpsimd_context()
257 fpsimd_sync_from_effective_state(current); in preserve_fpsimd_context()
299 current->thread.svcr &= ~SVCR_SM_MASK; in restore_fpsimd_context()
300 current->thread.fp_type = FP_STATE_FPSIMD; in restore_fpsimd_context()
313 __put_user_error(current->thread.uw.fpmr, &ctx->fpmr, err); in preserve_fpmr_context()
328 current->thread.uw.fpmr = fpmr; in restore_fpmr_context()
368 unsigned int vl = task_get_sve_vl(current); in preserve_sve_context()
371 if (thread_sm_enabled(&current->thread)) { in preserve_sve_context()
372 vl = task_get_sme_vl(current); in preserve_sve_context()
375 } else if (current->thread.fp_type == FP_STATE_SVE) { in preserve_sve_context()
[all …]
/linux/arch/mips/math-emu/
H A Ddsemul.c77 mm_context_t *mm_ctx = &current->mm->context; in alloc_emuframe()
116 pr_debug("allocate emuframe %d to %d\n", idx, current->pid); in alloc_emuframe()
128 pr_debug("free emuframe %d from %d\n", idx, current->pid); in free_emuframe()
180 fr_idx = atomic_read(&current->thread.bd_emu_frame); in dsemul_thread_rollback()
193 regs->cp0_epc = current->thread.bd_emu_branch_pc; in dsemul_thread_rollback()
195 regs->cp0_epc = current->thread.bd_emu_cont_pc; in dsemul_thread_rollback()
197 atomic_set(&current->thread.bd_emu_frame, BD_EMUFRAME_NONE); in dsemul_thread_rollback()
198 free_emuframe(fr_idx, current->mm); in dsemul_thread_rollback()
246 fr_idx = atomic_read(&current->thread.bd_emu_frame); in mips_dsemul()
273 ret = access_process_vm(current, fr_uaddr, &fr, sizeof(fr), in mips_dsemul()
[all …]
/linux/rust/macros/
H A Dfmt.rs54 let mut flush = |args: &mut TokenStream, current: &mut TokenStream| { in fmt()
55 let current = std::mem::take(current); in fmt()
56 if !current.is_empty() { in fmt() localVariable
58 let mut current = current.into_iter(); in fmt()
60 while let Some(tt) = current.next() { in fmt()
66 return (Some(acc), current.collect::<TokenStream>()); in fmt()
76 let mut current = TokenStream::new(); in fmt()
80 flush(&mut args, &mut current); in fmt()
53 let current = std::mem::take(current); fmt() localVariable
74 let mut current = TokenStream::new(); fmt() localVariable
[all...]
/linux/arch/um/kernel/
H A Dprocess.c79 arch_switch_to(current); in __switch_to()
81 return current->thread.prev_sched; in __switch_to()
86 struct pt_regs *regs = &current->thread.regs; in interrupt_end()
103 return task_pid_nr(current); in get_current_pid()
115 if (current->thread.prev_sched != NULL) in new_thread_handler()
116 schedule_tail(current->thread.prev_sched); in new_thread_handler()
117 current->thread.prev_sched = NULL; in new_thread_handler()
119 fn = current->thread.request.thread.proc; in new_thread_handler()
120 arg = current->thread.request.thread.arg; in new_thread_handler()
126 userspace(&current->thread.regs.regs); in new_thread_handler()
[all …]
/linux/arch/csky/kernel/probes/
H A Duprobes.c50 struct uprobe_task *utask = current->utask; in arch_uprobe_pre_xol()
52 utask->autask.saved_trap_no = current->thread.trap_no; in arch_uprobe_pre_xol()
53 current->thread.trap_no = UPROBE_TRAP_NR; in arch_uprobe_pre_xol()
57 user_enable_single_step(current); in arch_uprobe_pre_xol()
64 struct uprobe_task *utask = current->utask; in arch_uprobe_post_xol()
66 WARN_ON_ONCE(current->thread.trap_no != UPROBE_TRAP_NR); in arch_uprobe_post_xol()
67 current->thread.trap_no = utask->autask.saved_trap_no; in arch_uprobe_post_xol()
71 user_disable_single_step(current); in arch_uprobe_post_xol()
103 struct uprobe_task *utask = current->utask; in arch_uprobe_abort_xol()
105 current->thread.trap_no = utask->autask.saved_trap_no; in arch_uprobe_abort_xol()
[all …]
/linux/tools/iio/
H A Diio_utils.c31 char *current; in iioutils_break_up_name() local
43 current = strdup(full_name + strlen(prefix) + 1); in iioutils_break_up_name()
44 if (!current) in iioutils_break_up_name()
47 working = strtok(current, "_\0"); in iioutils_break_up_name()
49 free(current); in iioutils_break_up_name()
66 free(current); in iioutils_break_up_name()
321 struct iio_channel_info *current; in build_channel_array() local
385 current = &(*ci_array)[count++]; in build_channel_array()
421 current->scale = 1.0; in build_channel_array()
422 current->offset = 0; in build_channel_array()
[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
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,
49 curr4_crit Critical alert current(mA) setting for sum of current
[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/
H A Dvtime.h52 vtime_account_kernel(current); in vtime_account_guest_enter()
53 current->flags |= PF_VCPU; in vtime_account_guest_enter()
58 vtime_account_kernel(current); in vtime_account_guest_exit()
59 current->flags &= ~PF_VCPU; in vtime_account_guest_exit()
96 vtime_guest_enter(current); in vtime_account_guest_enter()
98 current->flags |= PF_VCPU; in vtime_account_guest_enter()
104 vtime_guest_exit(current); in vtime_account_guest_exit()
106 current->flags &= ~PF_VCPU; in vtime_account_guest_exit()
116 current->flags |= PF_VCPU; in vtime_account_guest_enter()
121 current->flags &= ~PF_VCPU; in vtime_account_guest_exit()
/linux/arch/loongarch/kernel/
H A Dsignal.c93 __put_user(get_fpr64(&current->thread.fpu.fpr[i], 0), in copy_fpu_to_sigcontext()
96 err |= __put_user(current->thread.fpu.fcc, fcc); in copy_fpu_to_sigcontext()
97 err |= __put_user(current->thread.fpu.fcsr, fcsr); in copy_fpu_to_sigcontext()
113 set_fpr64(&current->thread.fpu.fpr[i], 0, fpr_val); in copy_fpu_from_sigcontext()
115 err |= __get_user(current->thread.fpu.fcc, fcc); in copy_fpu_from_sigcontext()
116 err |= __get_user(current->thread.fpu.fcsr, fcsr); in copy_fpu_from_sigcontext()
130 err |= __put_user(get_fpr64(&current->thread.fpu.fpr[i], 0), in copy_lsx_to_sigcontext()
132 err |= __put_user(get_fpr64(&current->thread.fpu.fpr[i], 1), in copy_lsx_to_sigcontext()
135 err |= __put_user(current->thread.fpu.fcc, fcc); in copy_lsx_to_sigcontext()
136 err |= __put_user(current->thread.fpu.fcsr, fcsr); in copy_lsx_to_sigcontext()
[all …]
/linux/kernel/trace/
H A Dfgraph.c350 int curr_ret_stack = current->curr_ret_stack; in fgraph_reserve_data()
359 val = get_fgraph_entry(current, curr_ret_stack - 1); in fgraph_reserve_data()
360 data = &current->ret_stack[curr_ret_stack]; in fgraph_reserve_data()
369 current->ret_stack[curr_ret_stack - 1] = val; in fgraph_reserve_data()
373 current->curr_ret_stack = curr_ret_stack; in fgraph_reserve_data()
375 current->ret_stack[curr_ret_stack - 1] = val; in fgraph_reserve_data()
413 return ret_stack_get_task_var(current, gops->idx); in fgraph_get_task_var()
467 int offset = current->curr_ret_stack; in fgraph_retrieve_parent_data()
476 ret_stack = get_ret_stack(current, offset, &next_offset); in fgraph_retrieve_parent_data()
487 val = get_fgraph_entry(current, offset); in fgraph_retrieve_parent_data()
[all …]
/linux/arch/powerpc/math-emu/
H A Dmath.c332 op0 = (void *)&current->thread.TS_FPR((insn >> 21) & 0x1f); in do_mathemu()
333 op1 = (void *)&current->thread.TS_FPR((insn >> 16) & 0x1f); in do_mathemu()
334 op2 = (void *)&current->thread.TS_FPR((insn >> 11) & 0x1f); in do_mathemu()
338 op0 = (void *)&current->thread.TS_FPR((insn >> 21) & 0x1f); in do_mathemu()
339 op1 = (void *)&current->thread.TS_FPR((insn >> 16) & 0x1f); in do_mathemu()
340 op2 = (void *)&current->thread.TS_FPR((insn >> 6) & 0x1f); in do_mathemu()
344 op0 = (void *)&current->thread.TS_FPR((insn >> 21) & 0x1f); in do_mathemu()
345 op1 = (void *)&current->thread.TS_FPR((insn >> 16) & 0x1f); in do_mathemu()
346 op2 = (void *)&current->thread.TS_FPR((insn >> 11) & 0x1f); in do_mathemu()
347 op3 = (void *)&current->thread.TS_FPR((insn >> 6) & 0x1f); in do_mathemu()
[all …]

12345678910>>...111