Home
last modified time | relevance | path

Searched refs:thread (Results 1501 - 1525 of 2548) sorted by relevance

1...<<61626364656667686970>>...102

/kernel/linux/linux-5.10/arch/arm/mm/
H A Dfault.c172 tsk->thread.address = addr; in __do_user_fault()
173 tsk->thread.error_code = fsr; in __do_user_fault()
174 tsk->thread.trap_no = 14; in __do_user_fault()
/kernel/linux/linux-5.10/arch/powerpc/mm/book3s32/
H A Dmmu.c340 if (!current->thread.regs) in update_mmu_cache()
344 if (TRAP(current->thread.regs) != 0x300 && TRAP(current->thread.regs) != 0x400) in update_mmu_cache()
/kernel/linux/linux-5.10/arch/x86/include/asm/fpu/
H A Dinternal.h498 struct fpu *fpu = &current->thread.fpu; in __fpregs_load_activate()
524 * are saved in the current thread's FPU register state.
536 struct fpu *old_fpu = &prev->thread.fpu; in switch_fpu_prepare()
561 struct fpu *next_fpu = &next->thread.fpu; in switch_fpu_finish()
/kernel/linux/linux-5.10/arch/sparc/kernel/
H A Dprom_64.c382 int cpu, unsigned int *thread) in arch_find_n_match_cpu_physical_id()
415 if (thread) { in arch_find_n_match_cpu_physical_id()
418 /* On sparc64, the cpu thread information is obtained in arch_find_n_match_cpu_physical_id()
427 *thread = proc_id; in arch_find_n_match_cpu_physical_id()
381 arch_find_n_match_cpu_physical_id(struct device_node *cpun, int cpu, unsigned int *thread) arch_find_n_match_cpu_physical_id() argument
/kernel/linux/linux-5.10/arch/x86/ia32/
H A Dia32_signal.c175 unsafe_put_user(current->thread.trap_nr, &sc->trapno, Efault); in __unsafe_setup_sigcontext32()
176 unsafe_put_user(current->thread.error_code, &sc->err, Efault); in __unsafe_setup_sigcontext32()
187 unsafe_put_user(current->thread.cr2, &sc->cr2, Efault); in __unsafe_setup_sigcontext32()
/kernel/linux/linux-5.10/arch/arc/kernel/
H A Dentry.S59 jl.d [r14] ; kernel thread entry point
68 ; a kernel thread which is executed via JL above but always returns
169 st r12, [r11, THREAD_FAULT_ADDR] ; thread.fault_address
/kernel/linux/linux-5.10/tools/testing/selftests/x86/
H A Dfsgsbase.c241 printf("\tother thread: ARCH_SET_GS(0x%lx)%s -- sel is 0x%hx\n", in do_remote_base()
251 * that GSBASE == 0 (i.e. thread.gsbase == 0). in load_gs()
348 * thread.gsbase == 0. in threadproc()
354 errx(1, "helper thread got bad command"); in threadproc()
425 printf("[RUN]\tARCH_SET_GS(0), clear gs, then manipulate GSBASE in a different thread\n"); in test_unexpected_base()
589 pthread_t thread; in main() local
631 if (pthread_create(&thread, 0, threadproc, 0) != 0) in main()
669 ftx = 3; /* Kill the thread. */ in main()
672 if (pthread_join(thread, NULL) != 0) in main()
/kernel/linux/linux-6.6/arch/arc/kernel/
H A Dptrace.c98 struct callee_regs *tmp = (struct callee_regs *)tsk->thread.callee_reg; in task_callee_regs()
148 membuf_store(&to, target->thread.fault_address); // efa in genregs_get()
151 stop_pc_val = target->thread.fault_address; in genregs_get()
/kernel/linux/linux-6.6/arch/arm/mm/
H A Dfault.c200 tsk->thread.address = addr; in __do_user_fault()
201 tsk->thread.error_code = fsr; in __do_user_fault()
202 tsk->thread.trap_no = 14; in __do_user_fault()
/kernel/linux/linux-6.6/arch/sparc/kernel/
H A Dprom_64.c382 int cpu, unsigned int *thread) in arch_find_n_match_cpu_physical_id()
415 if (thread) { in arch_find_n_match_cpu_physical_id()
418 /* On sparc64, the cpu thread information is obtained in arch_find_n_match_cpu_physical_id()
427 *thread = proc_id; in arch_find_n_match_cpu_physical_id()
381 arch_find_n_match_cpu_physical_id(struct device_node *cpun, int cpu, unsigned int *thread) arch_find_n_match_cpu_physical_id() argument
/kernel/linux/linux-5.10/tools/perf/bench/
H A Depoll-ctl.c59 /* amount of fds to monitor, per thread */
69 pthread_t thread; member
77 OPT_UINTEGER('f', "nfds", &nfds, "Specify amount of file descriptors to monitor for each thread"),
266 ret = pthread_create(&w->thread, attrp, workerfn, in do_threads()
376 printinfo("main thread: toggling done\n"); in bench_epoll_ctl()
379 ret = pthread_join(worker[i].thread, NULL); in bench_epoll_ctl()
398 printf("[thread %2d] fdmap: %p [ add: %04ld; mod: %04ld; del: %04lds ops ]\n", in bench_epoll_ctl()
402 printf("[thread %2d] fdmap: %p ... %p [ add: %04ld ops; mod: %04ld ops; del: %04ld ops ]\n", in bench_epoll_ctl()
/kernel/linux/linux-5.10/tools/io_uring/
H A Dio_uring-bench.c73 pthread_t thread; member
103 static int sq_thread_poll = 0; /* use kernel submission/poller thread */
104 static int sq_thread_cpu = -1; /* pin above thread to this CPU */
306 * Only need to call io_uring_enter if we're not using SQ thread in submitter_fn()
322 * For non SQ thread poll, we already got the events we needed in submitter_fn()
323 * through the io_uring_enter() above. For SQ thread poll, we in submitter_fn()
560 pthread_create(&s->thread, NULL, submitter_fn, s); in main()
588 pthread_join(s->thread, &ret); in main()
/kernel/linux/linux-6.6/drivers/virt/acrn/
H A Dioreq.c167 * ioreq_task() is the execution entity of handler thread of an I/O client.
168 * The handler callback of the I/O client is called within the handler thread.
183 * clear_bit() - in handler thread (include ACRN userspace) in ioreq_task()
262 * In the default client, a user space thread waits on the in acrn_ioreq_client_wait()
408 * thread and call the handler to handle I/O requests.
442 client->thread = kthread_run(ioreq_task, client, "VM%u-%s", in acrn_ioreq_client_create()
444 if (IS_ERR(client->thread)) { in acrn_ioreq_client_create()
477 kthread_stop(client->thread); in acrn_ioreq_client_destroy()
/kernel/linux/linux-6.6/tools/perf/bench/
H A Depoll-ctl.c59 /* amount of fds to monitor, per thread */
69 pthread_t thread; member
77 OPT_UINTEGER('f', "nfds", &nfds, "Specify amount of file descriptors to monitor for each thread"),
276 ret = pthread_create(&w->thread, attrp, workerfn, in do_threads()
389 printinfo("main thread: toggling done\n"); in bench_epoll_ctl()
392 ret = pthread_join(worker[i].thread, NULL); in bench_epoll_ctl()
411 printf("[thread %2d] fdmap: %p [ add: %04ld; mod: %04ld; del: %04lds ops ]\n", in bench_epoll_ctl()
415 printf("[thread %2d] fdmap: %p ... %p [ add: %04ld ops; mod: %04ld ops; del: %04ld ops ]\n", in bench_epoll_ctl()
/kernel/linux/linux-6.6/tools/perf/util/
H A Dmaps.c9 #include "thread.h"
386 int maps__clone(struct thread *thread, struct maps *parent) in maps__clone() argument
388 struct maps *maps = thread__maps(thread); in maps__clone()
/kernel/linux/linux-6.6/tools/testing/selftests/x86/
H A Damx.c692 pthread_t thread; member
726 * The last thread's last unlock will be for in check_tiledata()
727 * thread 0's mutex. However, thread 0 will in check_tiledata()
739 * Return this thread's finfo, which is in check_tiledata()
740 * a unique value for this thread. in check_tiledata()
764 if (pthread_create(&finfo[i].thread, NULL, check_tiledata, &finfo[i])) in create_threads()
803 * This thread wakes up thread 0 in test_context_switch()
807 * the last thread wil in test_context_switch()
[all...]
H A Dtest_shadow_stack.c486 pthread_t thread; in test_userfaultfd() local
514 if (pthread_create(&thread, NULL, &uffd_thread, &uffd)) in test_userfaultfd()
520 if (pthread_join(thread, &res)) in test_userfaultfd()
H A Dfsgsbase.c241 printf("\tother thread: ARCH_SET_GS(0x%lx)%s -- sel is 0x%hx\n", in do_remote_base()
251 * that GSBASE == 0 (i.e. thread.gsbase == 0). in load_gs()
348 * thread.gsbase == 0. in threadproc()
354 errx(1, "helper thread got bad command"); in threadproc()
433 printf("[RUN]\tARCH_SET_GS(0), clear gs, then manipulate GSBASE in a different thread\n"); in test_unexpected_base()
597 pthread_t thread; in main() local
639 if (pthread_create(&thread, 0, threadproc, 0) != 0) in main()
677 ftx = 3; /* Kill the thread. */ in main()
680 if (pthread_join(thread, NULL) != 0) in main()
/third_party/musl/Benchmark/musl/
H A Dsocket_test.cpp396 pthread_t thread; in StartServer() local
398 pthread_create(&thread, nullptr, ThreadTaskClient, nullptr); in StartServer()
399 pthread_join(thread, &res); in StartServer()
/third_party/python/Lib/multiprocessing/
H A Dqueues.py32 # Queue type using a pipe, buffer and thread
164 # Start thread which transfers data from buffer to pipe
187 # Send sentinel to the thread queue object when garbage collected
196 debug('joining queue thread')
197 thread = twr()
198 if thread is not None:
199 thread.join()
200 debug('... queue thread joined')
202 debug('... queue thread already dead')
206 debug('telling queue thread t
[all...]
/third_party/skia/third_party/externals/angle2/src/libANGLE/renderer/gl/
H A DRendererGL.cpp376 std::thread::id threadID = std::this_thread::get_id(); in bindWorkerContext()
406 std::thread::id threadID = std::this_thread::get_id(); in unbindWorkerContext()
419 return std::min(16u, std::thread::hardware_concurrency()); in getMaxWorkerContexts()
/third_party/python/Lib/test/
H A Dtest_winreg.py266 thread = VeryActiveThread()
267 thread.start()
278 thread.join()
/third_party/skia/third_party/externals/swiftshader/third_party/marl/include/marl/
H A Dscheduler.h25 #include "thread.h"
32 #include <thread>
40 // Once bound to a thread, that thread can call marl::schedule() to enqueue
57 // Per-worker-thread settings.
62 // Initializer function to call after thread creation and before any work
63 // is run by the thread.
79 // allCores() returns a Config with a worker thread for each of the logical
103 // get() returns the scheduler bound to the current thread.
107 // bind() binds this scheduler to the current thread
472 Thread thread; global() member in marl::Scheduler::Worker
[all...]
/third_party/skia/third_party/externals/swiftshader/third_party/subzero/src/
H A DIceGlobalContext.h37 #include <thread>
59 /// block, to a translator thread.
150 /// ThreadContext contains thread-local data. This data can be
173 /// thread at a time. This is done by exclusively reserving the
177 /// The model is that a thread grabs the stream lock, then does an
179 /// the stream and do something with it, and finally the thread
315 /// thread-local copies of timer data have been merged into the global timer
322 /// The following methods affect only the calling thread's TLS timer data.
331 /// correspondingly the first sequence number that the emitter thread will
380 /// Translation thread startu
[all...]
/kernel/linux/linux-6.6/arch/powerpc/kvm/
H A Dbook3s_pr.c145 if (cpu_has_feature(CPU_FTR_ARCH_300) && (current->thread.fscr & FSCR_SCV)) in kvmppc_core_vcpu_load_pr()
152 current->thread.kvm_shadow_vcpu = vcpu->arch.shadow_vcpu; in kvmppc_core_vcpu_load_pr()
176 if (cpu_has_feature(CPU_FTR_ARCH_300) && (current->thread.fscr & FSCR_SCV)) in kvmppc_core_vcpu_put_pr()
806 struct thread_struct *t = &current->thread; in kvmppc_giveup_ext()
827 * registers into thread.fp_state.fpr[]. in kvmppc_giveup_ext()
836 if (current->thread.regs->msr & MSR_VEC) in kvmppc_giveup_ext()
858 mtspr(SPRN_TAR, current->thread.tar); in kvmppc_giveup_fac()
869 struct thread_struct *t = &current->thread; in kvmppc_handle_ext()
941 lost_ext = vcpu->arch.guest_owned_ext & ~current->thread.regs->msr; in kvmppc_handle_lost_ext()
961 current->thread in kvmppc_handle_lost_ext()
[all...]

Completed in 20 milliseconds

1...<<61626364656667686970>>...102