Searched refs:td (Results 51 - 75 of 1053) sorted by last modified time

1234567891011>>

/freebsd-11-stable/sys/compat/svr4/
H A Dsvr4_misc.c121 svr4_sys_setitimer(td, uap)
122 struct thread *td;
125 td->td_retval[0] = 0;
131 svr4_sys_wait(td, uap)
132 struct thread *td;
137 error = kern_wait(td, WAIT_ANY, &st, 0, NULL);
155 td->td_retval[1] = st;
164 svr4_sys_execv(td, uap)
165 struct thread *td;
173 CHECKALTEXIST(td, ua
[all...]
/freebsd-11-stable/sys/cam/scsi/
H A Dscsi_sg.c433 sgopen(struct cdev *dev, int flags, int fmt, struct thread *td) argument
446 error = securelevel_gt(td->td_ucred, 1);
469 sgclose(struct cdev *dev, int flag, int fmt, struct thread *td) argument
502 sgioctl(struct cdev *dev, u_long cmd, caddr_t arg, int flag, struct thread *td) argument
537 td->td_retval[0] = softc->sg_user_timeout;
/freebsd-11-stable/sys/sys/
H A Dsyscallsubr.h66 int kern___getcwd(struct thread *td, char *buf, enum uio_seg bufseg,
68 int kern_accept(struct thread *td, int s, struct sockaddr **name,
70 int kern_accept4(struct thread *td, int s, struct sockaddr **name,
72 int kern_accessat(struct thread *td, int fd, char *path,
74 int kern_adjtime(struct thread *td, struct timeval *delta,
76 int kern_alternate_path(struct thread *td, const char *prefix, const char *path,
78 int kern_bindat(struct thread *td, int dirfd, int fd, struct sockaddr *sa);
79 int kern_cap_ioctls_limit(struct thread *td, int fd, u_long *cmds,
81 int kern_cap_rights_limit(struct thread *td, int fd, cap_rights_t *rights);
82 int kern_chdir(struct thread *td, cha
[all...]
H A Dimgact.h100 void exec_cleanup(struct thread *td, struct vmspace *);
110 int pre_execve(struct thread *td, struct vmspace **oldvmspace);
111 void post_execve(struct thread *td, int error, struct vmspace *oldvmspace);
/freebsd-11-stable/sys/kern/
H A Dkern_exec.c119 static int do_execve(struct thread *td, struct image_args *args,
211 sys_execve(struct thread *td, struct execve_args *uap) argument
217 error = pre_execve(td, &oldvmspace);
223 error = kern_execve(td, &args, NULL, oldvmspace);
224 post_execve(td, error, oldvmspace);
236 sys_fexecve(struct thread *td, struct fexecve_args *uap) argument
242 error = pre_execve(td, &oldvmspace);
249 error = kern_execve(td, &args, NULL, oldvmspace);
251 post_execve(td, error, oldvmspace);
265 sys___mac_execve(struct thread *td, struc argument
287 pre_execve(struct thread *td, struct vmspace **oldvmspace) argument
308 post_execve(struct thread *td, int error, struct vmspace *oldvmspace) argument
337 kern_execve(struct thread *td, struct image_args *args, struct mac *mac_p, struct vmspace *oldvmspace) argument
353 do_execve(struct thread *td, struct image_args *args, struct mac *mac_p, struct vmspace *oldvmspace) argument
980 exec_cleanup(struct thread *td, struct vmspace *oldvmspace) argument
1275 exec_copyin_data_fds(struct thread *td, struct image_args *args, const void *data, size_t datalen, const int *fds, size_t fdslen) argument
1630 struct thread *td; local
[all...]
H A Dkern_sig.c106 static int killpg1(struct thread *td, int sig, int pgid, int all,
108 static int issignal(struct thread *td);
587 * Determine signal that should be delivered to thread td, the current
592 cursig(struct thread *td) argument
594 PROC_LOCK_ASSERT(td->td_proc, MA_OWNED);
595 mtx_assert(&td->td_proc->p_sigacts->ps_mtx, MA_OWNED);
596 THREAD_LOCK_ASSERT(td, MA_NOTOWNED);
597 return (SIGPENDING(td) ? issignal(td) : 0);
606 signotify(struct thread *td) argument
629 struct thread *td; local
683 kern_sigaction(struct thread *td, int sig, const struct sigaction *act, struct sigaction *oact, int flags) argument
835 sys_sigaction(struct thread *td, struct sigaction_args *uap) argument
863 freebsd4_sigaction(struct thread *td, struct freebsd4_sigaction_args *uap) argument
893 osigaction(struct thread *td, struct osigaction_args *uap) argument
927 osigreturn(struct thread *td, struct osigreturn_args *uap) argument
981 struct thread *td; local
1035 kern_sigprocmask(struct thread *td, int how, sigset_t *set, sigset_t *oset, int flags) argument
1109 sys_sigprocmask(struct thread *td, struct sigprocmask_args *uap) argument
1137 osigprocmask(struct thread *td, struct osigprocmask_args *uap) argument
1150 sys_sigwait(struct thread *td, struct sigwait_args *uap) argument
1178 sys_sigtimedwait(struct thread *td, struct sigtimedwait_args *uap) argument
1212 sys_sigwaitinfo(struct thread *td, struct sigwaitinfo_args *uap) argument
1235 proc_td_siginfo_capture(struct thread *td, siginfo_t *si) argument
1248 kern_sigtimedwait(struct thread *td, sigset_t waitset, ksiginfo_t *ksi, struct timespec *timeout) argument
1387 sys_sigpending(struct thread *td, struct sigpending_args *uap) argument
1406 osigpending(struct thread *td, struct osigpending_args *uap) argument
1433 osigvec(struct thread *td, struct osigvec_args *uap) argument
1471 osigblock(struct thread *td, struct osigblock_args *uap) argument
1487 osigsetmask(struct thread *td, struct osigsetmask_args *uap) argument
1509 sys_sigsuspend(struct thread *td, struct sigsuspend_args *uap) argument
1521 kern_sigsuspend(struct thread *td, sigset_t mask) argument
1583 osigsuspend(struct thread *td, struct osigsuspend_args *uap) argument
1601 osigstack(struct thread *td, struct osigstack_args *uap) argument
1634 sys_sigaltstack(struct thread *td, struct sigaltstack_args *uap) argument
1654 kern_sigaltstack(struct thread *td, stack_t *ss, stack_t *oss) argument
1690 killpg1(struct thread *td, int sig, int pgid, int all, ksiginfo_t *ksi) argument
1767 sys_kill(struct thread *td, struct kill_args *uap) argument
1817 sys_pdkill(struct thread *td, struct pdkill_args *uap) argument
1849 okillpg(struct thread *td, struct okillpg_args *uap) argument
1875 sys_sigqueue(struct thread *td, struct sigqueue_args *uap) argument
1885 kern_sigqueue(struct thread *td, pid_t pid, int signum, union sigval *value) argument
1968 postsig_done(int sig, struct thread *td, struct sigacts *ps) argument
1990 trapsignal(struct thread *td, ksiginfo_t *ksi) argument
2041 struct thread *td, *signal_td; local
2102 struct thread *td; local
2117 tdsignal(struct thread *td, int sig) argument
2128 tdksignal(struct thread *td, int sig, ksiginfo_t *ksi) argument
2135 tdsendsignal(struct proc *p, struct thread *td, int sig, ksiginfo_t *ksi) argument
2422 tdsigwakeup(struct thread *td, int sig, sig_t action, int intrval) argument
2503 sig_suspend_threads(struct thread *td, struct proc *p, int sending) argument
2554 ptracestop(struct thread *td, int sig, ksiginfo_t *si) argument
2670 struct thread *td; local
2698 tdsigcleanup(struct thread *td) argument
2746 struct thread *td; local
2788 struct thread *td; local
2816 issignal(struct thread *td) argument
3039 struct thread *td; local
3157 sigexit(struct thread *td, int sig) argument
3346 vnode_close_locked(struct thread *td, struct vnode *vp) argument
3361 corefile_open_last(struct thread *td, char *name, int indexpos, struct vnode **vpp) argument
3446 corefile_open(const char *comm, uid_t uid, pid_t pid, struct thread *td, int compress, struct vnode **vpp, char **namep) argument
3580 coredump(struct thread *td) argument
3721 nosys(struct thread *td, struct nosys_args *args) argument
[all...]
H A Dimgact_elf.c786 struct thread *td; local
836 td = curthread;
867 UIO_SYSSPACE, IO_NODELOCKED, td->td_ucred,
868 NOCRED, NULL, td);
1042 addr = round_page((vm_offset_t)vmspace->vm_daddr + lim_max(td,
1203 struct thread *td; member in struct:coredump_params
1286 p->active_cred, p->file_cred, NULL, p->td));
1340 locked = PROC_LOCKED(p->td->td_proc);
1342 PROC_UNLOCK(p->td->td_proc);
1351 PROC_LOCK(p->td
1372 coredump(struct thread *td, struct vnode *vp, off_t limit, int flags) argument
1632 prepare_notes(struct thread *td, struct note_info_list *list, size_t *sizep) argument
1692 puthdr(struct thread *td, void *hdr, size_t hdrsize, int numsegs, size_t notesz) argument
1960 struct thread *td; local
1988 struct thread *td; local
2009 struct thread *td; local
2025 struct thread *td; local
2068 struct thread *td; local
[all...]
H A Duipc_socket.c476 struct ucred *cred, struct thread *td)
516 so->so_fibnum = td->td_proc->p_fibnum;
531 error = (*prp->pr_usrreqs->pru_attach)(so, proto, td);
685 sobind(struct socket *so, struct sockaddr *nam, struct thread *td) argument
690 error = (*so->so_proto->pr_usrreqs->pru_bind)(so, nam, td);
696 sobindat(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument
701 error = (*so->so_proto->pr_usrreqs->pru_bindat)(fd, so, nam, td);
719 solisten(struct socket *so, int backlog, struct thread *td) argument
724 error = (*so->so_proto->pr_usrreqs->pru_listen)(so, backlog, td);
982 soconnect(struct socket *so, struct sockaddr *nam, struct thread *td) argument
475 socreate(int dom, struct socket **aso, int type, int proto, struct ucred *cred, struct thread *td) argument
989 soconnectat(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument
1053 sosend_dgram(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument
1218 sosend_generic(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument
1399 sosend(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument
3050 sopoll(struct socket *so, int events, struct ucred *active_cred, struct thread *td) argument
3063 sopoll_generic(struct socket *so, int events, struct ucred *active_cred, struct thread *td) argument
3155 pru_attach_notsupp(struct socket *so, int proto, struct thread *td) argument
3162 pru_bind_notsupp(struct socket *so, struct sockaddr *nam, struct thread *td) argument
3169 pru_bindat_notsupp(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument
3177 pru_connect_notsupp(struct socket *so, struct sockaddr *nam, struct thread *td) argument
3184 pru_connectat_notsupp(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument
3199 pru_control_notsupp(struct socket *so, u_long cmd, caddr_t data, struct ifnet *ifp, struct thread *td) argument
3214 pru_listen_notsupp(struct socket *so, int backlog, struct thread *td) argument
3242 pru_send_notsupp(struct socket *so, int flags, struct mbuf *m, struct sockaddr *addr, struct mbuf *control, struct thread *td) argument
3283 pru_sosend_notsupp(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument
3299 pru_sopoll_notsupp(struct socket *so, int events, struct ucred *cred, struct thread *td) argument
[all...]
H A Dinit_main.c389 null_fetch_syscall_args(struct thread *td __unused)
396 null_set_syscall_retval(struct thread *td __unused, int error __unused)
454 struct thread *td; local
461 td = &thread0;
505 td->td_tid = PID_MAX + 1;
506 LIST_INSERT_HEAD(TIDHASH(td->td_tid), td, td_hash);
507 td->td_state = TDS_RUNNING;
508 td->td_pri_class = PRI_TIMESHARE;
509 td
627 struct thread *td; local
733 struct thread *td; local
853 struct thread *td; local
896 struct thread *td; local
[all...]
/freebsd-11-stable/sys/compat/linux/
H A Dlinux_emul.c65 em_find(struct thread *td) argument
69 em = td->td_emuldata;
91 linux_proc_init(struct thread *td, struct thread *newtd, int flags) argument
119 p = td->td_proc;
125 em = em_find(td);
152 struct thread *td = curthread; local
158 td->td_tid, p->p_pid, p);
163 (p->p_sysent->sv_thread_detach)(td);
214 linux_common_execve(struct thread *td, struct image_args *eargs) argument
223 p = td
264 struct thread *td; local
319 linux_thread_dtor(void *arg __unused, struct thread *td) argument
334 linux_schedtail(struct thread *td) argument
[all...]
H A Dlinux_fork.c68 linux_fork(struct thread *td, struct linux_fork_args *args) argument
83 if ((error = fork1(td, &fr)) != 0)
88 linux_proc_init(td, td2, 0);
90 td->td_retval[0] = p2->p_pid;
104 linux_vfork(struct thread *td, struct linux_vfork_args *args) argument
119 if ((error = fork1(td, &fr)) != 0)
124 linux_proc_init(td, td2, 0);
126 td->td_retval[0] = p2->p_pid;
141 linux_clone_proc(struct thread *td, struct linux_clone_args *args) argument
187 error = fork1(td,
262 linux_clone_thread(struct thread *td, struct linux_clone_args *args) argument
400 linux_clone(struct thread *td, struct linux_clone_args *args) argument
410 linux_exit(struct thread *td, struct linux_exit_args *args) argument
433 linux_set_tid_address(struct thread *td, struct linux_set_tid_address_args *args) argument
451 linux_thread_detach(struct thread *td) argument
[all...]
/freebsd-11-stable/sys/compat/freebsd32/
H A Dfreebsd32_misc.c137 static int freebsd32_user_clock_nanosleep(struct thread *td, clockid_t clock_id,
163 freebsd32_wait4(struct thread *td, struct freebsd32_wait4_args *uap) argument
173 error = kern_wait(td, uap->pid, &status, uap->options, rup);
186 freebsd32_wait6(struct thread *td, struct freebsd32_wait6_args *uap) argument
203 error = kern_wait6(td, uap->idtype, PAIR32TO64(id_t, uap->id),
254 freebsd4_freebsd32_getfsstat(struct thread *td, argument
264 error = kern_getfsstat(td, &buf, size, &count, UIO_SYSSPACE, uap->mode);
278 td->td_retval[0] = count;
285 freebsd10_freebsd32_pipe(struct thread *td, argument
288 return (freebsd10_pipe(td, (struc
293 freebsd32_sigaltstack(struct thread *td, struct freebsd32_sigaltstack_args *uap) argument
419 freebsd32_execve(struct thread *td, struct freebsd32_execve_args *uap) argument
437 freebsd32_fexecve(struct thread *td, struct freebsd32_fexecve_args *uap) argument
457 freebsd32_mprotect(struct thread *td, struct freebsd32_mprotect_args *uap) argument
471 freebsd32_mmap(struct thread *td, struct freebsd32_mmap_args *uap) argument
487 freebsd6_freebsd32_mmap(struct thread *td, struct freebsd6_freebsd32_mmap_args *uap) argument
504 freebsd32_setitimer(struct thread *td, struct freebsd32_setitimer_args *uap) argument
528 freebsd32_getitimer(struct thread *td, struct freebsd32_getitimer_args *uap) argument
543 freebsd32_select(struct thread *td, struct freebsd32_select_args *uap) argument
566 freebsd32_pselect(struct thread *td, struct freebsd32_pselect_args *uap) argument
657 freebsd32_kevent(struct thread *td, struct freebsd32_kevent_args *uap) argument
697 freebsd32_gettimeofday(struct thread *td, struct freebsd32_gettimeofday_args *uap) argument
720 freebsd32_getrusage(struct thread *td, struct freebsd32_getrusage_args *uap) argument
776 freebsd32_readv(struct thread *td, struct freebsd32_readv_args *uap) argument
790 freebsd32_writev(struct thread *td, struct freebsd32_writev_args *uap) argument
804 freebsd32_preadv(struct thread *td, struct freebsd32_preadv_args *uap) argument
818 freebsd32_pwritev(struct thread *td, struct freebsd32_pwritev_args *uap) argument
1203 freebsd32_sendmsg(struct thread *td, struct freebsd32_sendmsg_args *uap) argument
1259 freebsd32_recvfrom(struct thread *td, struct freebsd32_recvfrom_args *uap) argument
1290 freebsd32_settimeofday(struct thread *td, struct freebsd32_settimeofday_args *uap) argument
1318 freebsd32_utimes(struct thread *td, struct freebsd32_utimes_args *uap) argument
1340 freebsd32_lutimes(struct thread *td, struct freebsd32_lutimes_args *uap) argument
1361 freebsd32_futimes(struct thread *td, struct freebsd32_futimes_args *uap) argument
1382 freebsd32_futimesat(struct thread *td, struct freebsd32_futimesat_args *uap) argument
1404 freebsd32_futimens(struct thread *td, struct freebsd32_futimens_args *uap) argument
1425 freebsd32_utimensat(struct thread *td, struct freebsd32_utimensat_args *uap) argument
1447 freebsd32_adjtime(struct thread *td, struct freebsd32_adjtime_args *uap) argument
1473 freebsd4_freebsd32_statfs(struct thread *td, struct freebsd4_freebsd32_statfs_args *uap) argument
1492 freebsd4_freebsd32_fstatfs(struct thread *td, struct freebsd4_freebsd32_fstatfs_args *uap) argument
1511 freebsd4_freebsd32_fhstatfs(struct thread *td, struct freebsd4_freebsd32_fhstatfs_args *uap) argument
1532 freebsd32_pread(struct thread *td, struct freebsd32_pread_args *uap) argument
1540 freebsd32_pwrite(struct thread *td, struct freebsd32_pwrite_args *uap) argument
1549 ofreebsd32_lseek(struct thread *td, struct ofreebsd32_lseek_args *uap) argument
1557 freebsd32_lseek(struct thread *td, struct freebsd32_lseek_args *uap) argument
1572 freebsd32_truncate(struct thread *td, struct freebsd32_truncate_args *uap) argument
1580 freebsd32_ftruncate(struct thread *td, struct freebsd32_ftruncate_args *uap) argument
1588 ofreebsd32_getdirentries(struct thread *td, struct ofreebsd32_getdirentries_args *uap) argument
1610 freebsd32_getdirentries(struct thread *td, struct freebsd32_getdirentries_args *uap) argument
1631 freebsd6_freebsd32_pread(struct thread *td, struct freebsd6_freebsd32_pread_args *uap) argument
1639 freebsd6_freebsd32_pwrite(struct thread *td, struct freebsd6_freebsd32_pwrite_args *uap) argument
1647 freebsd6_freebsd32_lseek(struct thread *td, struct freebsd6_freebsd32_lseek_args *uap) argument
1662 freebsd6_freebsd32_truncate(struct thread *td, struct freebsd6_freebsd32_truncate_args *uap) argument
1670 freebsd6_freebsd32_ftruncate(struct thread *td, struct freebsd6_freebsd32_ftruncate_args *uap) argument
1685 freebsd32_do_sendfile(struct thread *td, struct freebsd32_sendfile_args *uap, int compat) argument
1764 freebsd4_freebsd32_sendfile(struct thread *td, struct freebsd4_freebsd32_sendfile_args *uap) argument
1773 freebsd32_sendfile(struct thread *td, struct freebsd32_sendfile_args *uap) argument
1825 freebsd32_stat(struct thread *td, struct freebsd32_stat_args *uap) argument
1842 ofreebsd32_stat(struct thread *td, struct ofreebsd32_stat_args *uap) argument
1859 freebsd32_fstat(struct thread *td, struct freebsd32_fstat_args *uap) argument
1875 ofreebsd32_fstat(struct thread *td, struct ofreebsd32_fstat_args *uap) argument
1891 freebsd32_fstatat(struct thread *td, struct freebsd32_fstatat_args *uap) argument
1907 freebsd32_lstat(struct thread *td, struct freebsd32_lstat_args *uap) argument
1924 ofreebsd32_lstat(struct thread *td, struct ofreebsd32_lstat_args *uap) argument
1941 freebsd32_sysctl(struct thread *td, struct freebsd32_sysctl_args *uap) argument
1971 freebsd32_jail(struct thread *td, struct freebsd32_jail_args *uap) argument
2032 freebsd32_jail_set(struct thread *td, struct freebsd32_jail_set_args *uap) argument
2050 freebsd32_jail_get(struct thread *td, struct freebsd32_jail_get_args *uap) argument
2077 freebsd32_sigaction(struct thread *td, struct freebsd32_sigaction_args *uap) argument
2105 freebsd4_freebsd32_sigaction(struct thread *td, struct freebsd4_freebsd32_sigaction_args *uap) argument
2143 ofreebsd32_sigaction(struct thread *td, struct ofreebsd32_sigaction_args *uap) argument
2174 ofreebsd32_sigprocmask(struct thread *td, struct ofreebsd32_sigprocmask_args *uap) argument
2187 ofreebsd32_sigpending(struct thread *td, struct ofreebsd32_sigpending_args *uap) argument
2208 ofreebsd32_sigvec(struct thread *td, struct ofreebsd32_sigvec_args *uap) argument
2242 ofreebsd32_sigblock(struct thread *td, struct ofreebsd32_sigblock_args *uap) argument
2254 ofreebsd32_sigsetmask(struct thread *td, struct ofreebsd32_sigsetmask_args *uap) argument
2266 ofreebsd32_sigsuspend(struct thread *td, struct ofreebsd32_sigsuspend_args *uap) argument
2281 ofreebsd32_sigstack(struct thread *td, struct ofreebsd32_sigstack_args *uap) argument
2316 freebsd32_nanosleep(struct thread *td, struct freebsd32_nanosleep_args *uap) argument
2324 freebsd32_clock_nanosleep(struct thread *td, struct freebsd32_clock_nanosleep_args *uap) argument
2335 freebsd32_user_clock_nanosleep(struct thread *td, clockid_t clock_id, int flags, const struct timespec32 *ua_rqtp, struct timespec32 *ua_rmtp) argument
2362 freebsd32_clock_gettime(struct thread *td, struct freebsd32_clock_gettime_args *uap) argument
2379 freebsd32_clock_settime(struct thread *td, struct freebsd32_clock_settime_args *uap) argument
2396 freebsd32_clock_getres(struct thread *td, struct freebsd32_clock_getres_args *uap) argument
2414 freebsd32_ktimer_create(struct thread *td, struct freebsd32_ktimer_create_args *uap) argument
2442 freebsd32_ktimer_settime(struct thread *td, struct freebsd32_ktimer_settime_args *uap) argument
2463 freebsd32_ktimer_gettime(struct thread *td, struct freebsd32_ktimer_gettime_args *uap) argument
2479 freebsd32_clock_getcpuclockid2(struct thread *td, struct freebsd32_clock_getcpuclockid2_args *uap) argument
2493 freebsd32_thr_new(struct thread *td, struct freebsd32_thr_new_args *uap) argument
2526 freebsd32_thr_suspend(struct thread *td, struct freebsd32_thr_suspend_args *uap) argument
2570 freebsd32_sigqueue(struct thread *td, struct freebsd32_sigqueue_args *uap) argument
2589 freebsd32_sigtimedwait(struct thread *td, struct freebsd32_sigtimedwait_args *uap) argument
2631 freebsd32_sigwaitinfo(struct thread *td, struct freebsd32_sigwaitinfo_args *uap) argument
2656 freebsd32_cpuset_setid(struct thread *td, struct freebsd32_cpuset_setid_args *uap) argument
2665 freebsd32_cpuset_getid(struct thread *td, struct freebsd32_cpuset_getid_args *uap) argument
2674 freebsd32_cpuset_getaffinity(struct thread *td, struct freebsd32_cpuset_getaffinity_args *uap) argument
2683 freebsd32_cpuset_setaffinity(struct thread *td, struct freebsd32_cpuset_setaffinity_args *uap) argument
2692 freebsd32_nmount(struct thread *td, struct freebsd32_nmount_args *uap) argument
3021 freebsd32_kldstat(struct thread *td, struct freebsd32_kldstat_args *uap) argument
3054 freebsd32_posix_fallocate(struct thread *td, struct freebsd32_posix_fallocate_args *uap) argument
3065 freebsd32_posix_fadvise(struct thread *td, struct freebsd32_posix_fadvise_args *uap) argument
3102 freebsd32_procctl(struct thread *td, struct freebsd32_procctl_args *uap) argument
3192 freebsd32_fcntl(struct thread *td, struct freebsd32_fcntl_args *uap) argument
3220 freebsd32_ppoll(struct thread *td, struct freebsd32_ppoll_args *uap) argument
3248 freebsd32_sched_rr_get_interval(struct thread *td, struct freebsd32_sched_rr_get_interval_args *uap) argument
[all...]
/freebsd-11-stable/sys/compat/cloudabi/
H A Dcloudabi_proc.c46 cloudabi_sys_proc_exec(struct thread *td, argument
53 error = pre_execve(td, &oldvmspace);
56 error = exec_copyin_data_fds(td, &args, uap->data, uap->data_len,
60 error = kern_execve(td, &args, NULL, oldvmspace);
62 post_execve(td, error, oldvmspace);
67 cloudabi_sys_proc_exit(struct thread *td, argument
71 exit1(td, uap->rval, 0);
76 cloudabi_sys_proc_fork(struct thread *td, argument
88 error = fork1(td, &fr);
92 td
97 cloudabi_sys_proc_raise(struct thread *td, struct cloudabi_sys_proc_raise_args *uap) argument
[all...]
/freebsd-11-stable/sys/fs/udf/
H A Dudf_vfsops.c192 struct thread *td; local
199 td = curthread;
228 NDINIT(ndp, LOOKUP, FOLLOW | LOCKLEAF, UIO_SYSSPACE, fspec, td);
240 error = VOP_ACCESS(devvp, VREAD, td->td_ucred, td);
242 error = priv_check(td, PRIV_VFS_MOUNT_PERM);
587 struct thread *td; local
614 td = curthread;
619 if ((error = udf_allocv(mp, &vp, td))) {
636 error = vfs_hash_insert(vp, ino, flags, td, vp
[all...]
/freebsd-11-stable/sys/geom/part/
H A Dg_part.c2118 g_part_ioctl(struct g_provider *pp, u_long cmd, void *data, int fflag, struct thread *td) argument
2123 return G_PART_IOCTL(table, pp, cmd, data, fflag, td);
/freebsd-11-stable/contrib/llvm-project/openmp/runtime/src/
H A Dkmp.h2332 #define TASK_DEQUE_SIZE(td) ((td).td_deque_size)
2333 #define TASK_DEQUE_MASK(td) ((td).td_deque_size - 1)
2336 kmp_base_thread_data_t td; member in union:kmp_thread_data
/freebsd-11-stable/sys/cddl/contrib/opensolaris/uts/common/fs/zfs/
H A Dzfs_vfsops.c179 struct thread *td; local
186 td = curthread;
194 id = td->td_ucred->cr_ruid;
197 id = td->td_ucred->cr_rgid;
1782 kthread_t *td = curthread; local
1784 cred_t *cr = td->td_ucred;
1819 if (!prison_allow(td->td_ucred, PR_ALLOW_MOUNT_ZFS))
1863 VOP_ACCESS(mvp, VWRITE, cr, td) != 0) {
2126 kthread_t *td = curthread; local
2129 cred_t *cr = td
[all...]
/freebsd-11-stable/sys/dev/netmap/
H A Dnetmap_legacy.c355 struct thread *td)
376 error = netmap_ioctl(priv, NIOCCTRL, (caddr_t)hdr, td,
419 error = ifioctl(&so, cmd, data, td);
354 netmap_ioctl_legacy(struct netmap_priv_d *priv, u_long cmd, caddr_t data, struct thread *td) argument
/freebsd-11-stable/sys/dev/usb/
H A Dusb_freebsd_loader.h58 #define USB_TD_GET_PROC(td) (td)->td_proc
59 #define USB_PROC_GET_GID(td) (td)->p_pgid
H A Dusb_freebsd.h59 #define USB_TD_GET_PROC(td) (td)->td_proc
60 #define USB_PROC_GET_GID(td) (td)->p_pgid
H A Dusb_dev.c872 usb_open(struct cdev *dev, int fflags, int devtype, struct thread *td) argument
1010 struct thread *td)
1029 f->async_p = USB_TD_GET_PROC(td);
1057 usb_ioctl(struct cdev *dev, u_long cmd, caddr_t addr, int fflag, struct thread* td) argument
1087 err = usb_ioctl_f_sub(f, cmd, addr, td);
1091 err = usb_ioctl_f_sub(f, cmd, addr, td);
1300 usb_poll(struct cdev* dev, int events, struct thread* td) argument
1351 selrecord(td, &f->selinfo);
1390 selrecord(td, &f->selinfo);
1670 struct thread *td)
1009 usb_ioctl_f_sub(struct usb_fifo *f, u_long cmd, void *addr, struct thread *td) argument
1669 usb_static_ioctl(struct cdev *dev, u_long cmd, caddr_t data, int fflag, struct thread *td) argument
[all...]
/freebsd-11-stable/usr.bin/clang/llvm-objcopy/
H A DMakefile30 ${hdr}.inc: ${LLVM_BASE}/${SRCDIR}/${hdr}.td
33 -d ${.TARGET}.d -o ${.TARGET} ${LLVM_BASE}/${SRCDIR}/${hdr}.td
/freebsd-11-stable/lib/clang/libllvm/
H A DMakefile1630 llvm/IR/Attributes.inc: ${LLVM_SRCS}/include/llvm/IR/Attributes.td
1633 ${LLVM_SRCS}/include/llvm/IR/Attributes.td
1636 llvm/IR/IntrinsicEnums.inc: ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td
1639 ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td
1642 llvm/IR/IntrinsicImpl.inc: ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td
1645 ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td
1652 llvm/IR/Intrinsics${arch:H}.h: ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td
1655 ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td
1659 AttributesCompatFunc.inc: ${LLVM_SRCS}/lib/IR/AttributesCompatFunc.td
1662 ${LLVM_SRCS}/lib/IR/AttributesCompatFunc.td
[all...]
/freebsd-11-stable/lib/clang/libclang/
H A DMakefile701 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td
704 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td
708 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td
711 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td
715 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td
718 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td
722 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td
725 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td
728 clang/AST/AttrImpl.inc: ${CLANG_SRCS}/include/clang/Basic/Attr.td
731 ${CLANG_SRCS}/include/clang/Basic/Attr.td
[all...]
/freebsd-11-stable/lib/clang/headers/
H A DMakefile162 arm_fp16.h: ${CLANG_SRCS}/include/clang/Basic/arm_fp16.td
165 -o ${.TARGET} ${CLANG_SRCS}/include/clang/Basic/arm_fp16.td
167 arm_mve.h: ${CLANG_SRCS}/include/clang/Basic/arm_mve.td
170 -o ${.TARGET} ${CLANG_SRCS}/include/clang/Basic/arm_mve.td
172 arm_neon.h: ${CLANG_SRCS}/include/clang/Basic/arm_neon.td
175 -o ${.TARGET} ${CLANG_SRCS}/include/clang/Basic/arm_neon.td

Completed in 226 milliseconds

1234567891011>>