Searched refs:thread (Results 176 - 200 of 734) sorted by relevance

1234567891011>>

/linux-master/arch/riscv/kernel/
H A Dkernel_mode_vector.c23 WRITE_ONCE(current->thread.riscv_v_flags, flags);
86 return &current->thread.riscv_v_flags;
128 kvstate = &current->thread.kernel_vstate;
147 uvstate = &current->thread.vstate;
171 struct __riscv_v_ext_state *vstate = &current->thread.kernel_vstate;
218 riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));
/linux-master/tools/testing/selftests/kvm/
H A Dhardware_disable_test.c62 static inline void check_create_thread(pthread_t *thread, pthread_attr_t *attr, argument
67 r = pthread_create(thread, attr, f, arg);
68 TEST_ASSERT(r == 0, "%s: failed to create thread", __func__);
71 static inline void check_set_affinity(pthread_t thread, cpu_set_t *cpu_set) argument
75 r = pthread_setaffinity_np(thread, sizeof(cpu_set_t), cpu_set);
79 static inline void check_join(pthread_t thread, void **retval) argument
83 r = pthread_join(thread, retval);
84 TEST_ASSERT(r == 0, "%s: failed to join thread", __func__);
/linux-master/tools/perf/tests/
H A Dsymbols.c9 #include "thread.h"
17 struct thread *thread; member in struct:test_info
28 /* Create a dummy thread */
29 ti->thread = machine__findnew_thread(ti->machine, 100, 100);
30 if (!ti->thread) {
40 thread__put(ti->thread);
100 PROT_EXEC, 0, NULL, filename, ti->thread);
H A Dthread-maps-share.c4 #include "thread.h"
12 /* thread group */
13 struct thread *leader;
14 struct thread *t1, *t2, *t3;
18 struct thread *other, *other_leader;
22 * This test create 2 processes abstractions (struct thread)
26 * thread group (pid: 0, tids: 0, 1, 2, 3)
39 /* and create 1 separated process, without thread leader */
78 /* release thread group */
100 DEFINE_SUITE("Share thread map
[all...]
H A Dhists_common.c11 #include "util/thread.h"
96 struct thread *thread; local
98 thread = machine__findnew_thread(machine, fake_threads[i].pid,
100 if (thread == NULL)
103 thread__set_comm(thread, fake_threads[i].comm, 0);
104 thread__put(thread);
185 i, thread__comm_str(he->thread),
214 i, thread__comm_str(he->thread), thread__tid(he->thread),
[all...]
/linux-master/drivers/acpi/acpica/
H A Dutstate.c109 * to track per-thread info during method execution
129 state->thread.thread_id = acpi_os_get_thread_id();
131 /* Check for invalid thread ID - zero is very bad, it will break things */
133 if (!state->thread.thread_id) {
135 state->thread.thread_id = (acpi_thread_id) 1;
/linux-master/tools/testing/selftests/ptrace/
H A Dvmaccess.c18 static void *thread(void *arg) function
32 pthread_create(&pt, NULL, thread, NULL);
53 pthread_create(&pt, NULL, thread, NULL);
/linux-master/arch/csky/kernel/
H A Dprocess.c42 save_to_user_fp(&p->thread.user_fp);
48 /* setup thread.sp for switch_to !!! */
49 p->thread.sp = (unsigned long)childstack;
75 memcpy(fpu, &current->thread.user_fp, sizeof(*fpu));
/linux-master/tools/perf/arch/riscv/util/
H A Dunwind-libdw.c10 bool libdw__arch_set_initial_registers(Dwfl_Thread *thread, void *arg) argument
54 dwfl_thread_state_register_pc(thread, REG(PC));
56 return dwfl_thread_state_registers(thread, 0, PERF_REG_RISCV_MAX,
/linux-master/tools/perf/arch/s390/util/
H A Dunwind-libdw.c11 bool libdw__arch_set_initial_registers(Dwfl_Thread *thread, void *arg) argument
63 dwfl_thread_state_register_pc(thread, dwarf_regs[65]);
64 return dwfl_thread_state_registers(thread, 0, 32, dwarf_regs);
/linux-master/tools/perf/arch/arm64/util/
H A Dunwind-libdw.c8 bool libdw__arch_set_initial_registers(Dwfl_Thread *thread, void *arg) argument
53 if (!dwfl_thread_state_registers(thread, 0, PERF_REG_ARM64_MAX,
58 dwfl_thread_state_register_pc(thread, dwarf_pc);
/linux-master/tools/perf/arch/loongarch/util/
H A Dunwind-libdw.c10 bool libdw__arch_set_initial_registers(Dwfl_Thread *thread, void *arg) argument
54 dwfl_thread_state_register_pc(thread, REG(PC));
56 return dwfl_thread_state_registers(thread, 0, PERF_REG_LOONGARCH_MAX, dwarf_regs);
/linux-master/arch/arm64/include/asm/
H A Dthread_info.h49 ((unsigned long)(tsk->thread.cpu_context.pc))
51 ((unsigned long)(tsk->thread.cpu_context.sp))
53 ((unsigned long)(tsk->thread.cpu_context.fp))
/linux-master/drivers/md/dm-vdo/
H A DMakefile37 thread-device.o \
38 thread-registry.o \
39 thread-utils.o \
/linux-master/tools/perf/
H A Dbuiltin-sched.c11 #include "util/thread.h"
69 pthread_t thread; member in struct:task_desc
113 struct thread *thread; member in struct:work_atoms
179 struct thread **curr_thread;
234 /* per thread run time data */
268 struct thread *last_thread;
275 static struct thread **idle_threads;
670 err = pthread_create(&task->thread, &attr, thread_func, parms);
688 err = pthread_join(task->thread, NUL
922 thread__init_runtime(struct thread *thread) argument
936 thread__get_runtime(struct thread *thread) argument
968 thread_atoms_search(struct rb_root_cached *root, struct thread *thread, struct list_head *sort_list) argument
1021 thread_atoms_insert(struct perf_sched *sched, struct thread *thread) argument
1180 struct thread *thread = machine__findnew_thread(machine, -1, pid); local
1514 thread__has_color(struct thread *thread) argument
1526 struct thread *thread = machine__findnew_thread(machine, pid, tid); local
1781 struct thread *thread; local
1929 timehist_get_commstr(struct thread *thread) argument
2011 timehist_print_sample(struct perf_sched *sched, struct evsel *evsel, struct perf_sample *sample, struct addr_location *al, struct thread *thread, u64 t, const char state) argument
2163 struct thread *thread; local
2207 init_idle_thread(struct thread *thread) argument
2323 struct thread *thread; local
2365 timehist_skip_sample(struct perf_sched *sched, struct thread *thread, struct evsel *evsel, struct perf_sample *sample) argument
2394 struct thread *thread; local
2438 struct thread *thread; local
2468 struct thread *thread; local
2522 struct thread *thread; local
2552 struct thread *thread; local
[all...]
/linux-master/drivers/media/usb/pvrusb2/
H A Dpvrusb2-dvb.h29 struct task_struct *thread; member in struct:pvr2_dvb_adapter
/linux-master/drivers/media/pci/saa7134/
H A Dsaa7134-tvaudio.c304 if (dev->thread.scan1 == dev->thread.scan2 &&
314 return dev->thread.scan1 != dev->thread.scan2;
477 dev->thread.scan1 = dev->thread.scan2;
478 audio_dbg(1, "tvaudio thread scan start [%d]\n",
479 dev->thread.scan1);
518 if (dev->thread.scan1 != dev->thread
[all...]
/linux-master/arch/xtensa/include/asm/
H A Dstacktrace.h27 sp = task->thread.sp;
/linux-master/tools/testing/selftests/kvm/include/
H A Duserfaultfd_util.h26 pthread_t thread; member in struct:uffd_desc
/linux-master/arch/riscv/include/asm/
H A Dentry-common.h19 riscv_v_vstate_restore(&current->thread.vstate, regs);
H A Dvector.h35 return READ_ONCE(current->thread.riscv_v_flags);
207 return !!(task->thread.riscv_v_flags & RISCV_PREEMPT_V_DIRTY);
212 return !!(task->thread.riscv_v_flags & RISCV_PREEMPT_V_NEED_RESTORE);
218 task->thread.riscv_v_flags &= ~RISCV_PREEMPT_V_DIRTY;
224 task->thread.riscv_v_flags |= RISCV_PREEMPT_V_NEED_RESTORE;
229 return !!(task->thread.riscv_v_flags & RISCV_PREEMPT_V);
247 __riscv_v_vstate_save(&prev->thread.kernel_vstate,
248 prev->thread.kernel_vstate.datap);
253 riscv_v_vstate_save(&prev->thread.vstate, regs);
/linux-master/arch/x86/include/asm/fpu/
H A Dsched.h30 * are saved in the current thread's FPU register state.
44 struct fpu *old_fpu = &old->thread.fpu;
/linux-master/io_uring/
H A Dsqpoll.h11 struct task_struct *thread; member in struct:io_sq_data
/linux-master/arch/x86/kernel/
H A Dprocess_64.c180 * user thread without the need of loading a user thread GS with:
184 * - Accessing the GS segment base address for a user thread as
230 * Saves the FS or GS base for an outgoing thread if FSGSBASE extensions are
268 prev_p->thread.fsbase = 0;
270 prev_p->thread.gsbase = 0;
276 savesegment(fs, task->thread.fsindex);
277 savesegment(gs, task->thread.gsindex);
284 task->thread.fsbase = rdfsbase();
285 task->thread
[all...]
H A Dptrace.c195 retval = task->thread.gs;
233 task->thread.gs = value;
263 return task->thread.fsindex;
269 return task->thread.gsindex;
275 return task->thread.ds;
281 return task->thread.es;
310 task->thread.fsindex = value;
313 task->thread.gsindex = value;
316 task->thread.ds = value;
319 task->thread
476 struct thread_struct *thread = &(current->thread); local
562 struct thread_struct *thread = &tsk->thread; local
613 struct thread_struct *thread = &tsk->thread; local
672 struct thread_struct *thread = &tsk->thread; local
[all...]

Completed in 222 milliseconds

1234567891011>>