/linux-master/arch/riscv/kernel/ |
H A D | kernel_mode_vector.c | 23 WRITE_ONCE(current->thread.riscv_v_flags, flags); 86 return ¤t->thread.riscv_v_flags; 128 kvstate = ¤t->thread.kernel_vstate; 147 uvstate = ¤t->thread.vstate; 171 struct __riscv_v_ext_state *vstate = ¤t->thread.kernel_vstate; 218 riscv_v_vstate_save(¤t->thread.vstate, task_pt_regs(current));
|
/linux-master/tools/testing/selftests/kvm/ |
H A D | hardware_disable_test.c | 62 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 D | symbols.c | 9 #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 D | thread-maps-share.c | 4 #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 D | hists_common.c | 11 #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 D | utstate.c | 109 * 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 D | vmaccess.c | 18 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 D | process.c | 42 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, ¤t->thread.user_fp, sizeof(*fpu));
|
/linux-master/tools/perf/arch/riscv/util/ |
H A D | unwind-libdw.c | 10 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 D | unwind-libdw.c | 11 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 D | unwind-libdw.c | 8 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 D | unwind-libdw.c | 10 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 D | thread_info.h | 49 ((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 D | Makefile | 37 thread-device.o \ 38 thread-registry.o \ 39 thread-utils.o \
|
/linux-master/tools/perf/ |
H A D | builtin-sched.c | 11 #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 D | pvrusb2-dvb.h | 29 struct task_struct *thread; member in struct:pvr2_dvb_adapter
|
/linux-master/drivers/media/pci/saa7134/ |
H A D | saa7134-tvaudio.c | 304 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 D | stacktrace.h | 27 sp = task->thread.sp;
|
/linux-master/tools/testing/selftests/kvm/include/ |
H A D | userfaultfd_util.h | 26 pthread_t thread; member in struct:uffd_desc
|
/linux-master/arch/riscv/include/asm/ |
H A D | entry-common.h | 19 riscv_v_vstate_restore(¤t->thread.vstate, regs);
|
H A D | vector.h | 35 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 D | sched.h | 30 * are saved in the current thread's FPU register state. 44 struct fpu *old_fpu = &old->thread.fpu;
|
/linux-master/io_uring/ |
H A D | sqpoll.h | 11 struct task_struct *thread; member in struct:io_sq_data
|
/linux-master/arch/x86/kernel/ |
H A D | process_64.c | 180 * 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 D | ptrace.c | 195 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...] |