| /netbsd-src/external/gpl3/gcc/dist/libgomp/config/nvptx/ |
| H A D | bar.c | 69 unsigned int waiters in futex_wait() local
70 = __atomic_add_fetch (&bar->waiters, 1, MEMMODEL_ACQ_REL); in futex_wait()
71 if (waiters == 0) in futex_wait()
73 unsigned int waiter_id = waiters; in futex_wait()
75 if (waiters > 1) in futex_wait()
78 asm volatile ("bar.sync 1, %0;" : : "r" (32 * waiters)); in futex_wait()
81 asm volatile ("bar.sync 1, %0;" : : "r" (32 * waiters)); in futex_wait()
89 asm volatile ("bar.sync 1, %0;" : : "r" (32 * (waiters + 1))); in futex_wait()
93 = __atomic_load_n (&bar->waiters, MEMMODEL_ACQUIRE); in futex_wait()
96 asm volatile ("bar.sync 1, %0;" : : "r" (32 * (waiters + 1))); in futex_wait()
[all …]
|
| H A D | bar.h | 41 unsigned waiters; member
62 bar->waiters = 0; in gomp_barrier_init()
|
| /netbsd-src/external/bsd/tmux/dist/ |
| H A D | cmd-wait-for.c | 54 TAILQ_HEAD(, wait_item) waiters;
94 TAILQ_INIT(&wc->waiters); in cmd_wait_for_add()
109 if (!TAILQ_EMPTY(&wc->waiters) || !wc->woken) in cmd_wait_for_remove()
148 if (TAILQ_EMPTY(&wc->waiters) && !wc->woken) { in cmd_wait_for_signal()
155 TAILQ_FOREACH_SAFE(wi, &wc->waiters, entry, wi1) { in cmd_wait_for_signal()
158 TAILQ_REMOVE(&wc->waiters, wi, entry); in cmd_wait_for_signal()
190 TAILQ_INSERT_TAIL(&wc->waiters, wi, entry); in cmd_wait_for_wait()
250 TAILQ_FOREACH_SAFE(wi, &wc->waiters, entry, wi1) { in cmd_wait_for_flush()
252 TAILQ_REMOVE(&wc->waiters, wi, entry); in cmd_wait_for_flush()
|
| /netbsd-src/sys/external/bsd/drm2/dist/drm/radeon/ |
| H A D | radeon_semaphore.c | 55 (*semaphore)->waiters = 0; in radeon_semaphore_create()
71 --semaphore->waiters; in radeon_semaphore_emit_signal()
88 ++semaphore->waiters; in radeon_semaphore_emit_wait()
104 if ((*semaphore)->waiters > 0) { in radeon_semaphore_free()
|
| H A D | radeon_trace.h | 178 __field(signed, waiters)
184 __entry->waiters = sem->waiters;
189 __entry->waiters, __entry->gpu_addr)
|
| H A D | radeon.h | 619 signed waiters; member
|
| /netbsd-src/lib/librumpuser/ |
| H A D | rumpfiber.c | 678 struct waithead waiters; member
692 TAILQ_INIT(&mtx->waiters); in rumpuser_mutex_init()
711 wait(&mtx->waiters, 0); in rumpuser_mutex_enter()
749 wakeup_one(&mtx->waiters); in rumpuser_mutex_exit()
757 assert(TAILQ_EMPTY(&mtx->waiters) && mtx->o == NULL); in rumpuser_mutex_destroy()
905 struct waithead waiters; member
916 TAILQ_INIT(&cv->waiters); in rumpuser_cv_init()
958 wait(&cv->waiters, 0); in rumpuser_cv_wait()
969 wait(&cv->waiters, 0); in rumpuser_cv_wait_nowrap()
983 rv = wait(&cv->waiters, sec * 1000 + nsec / (1000*1000)); in rumpuser_cv_timedwait()
[all …]
|
| /netbsd-src/sys/external/bsd/vchiq/dist/interface/compat/ |
| H A D | vchi_bsd.c | 157 s->waiters++; in down()
159 s->waiters--; in down()
173 s->waiters++; in down_interruptible()
175 s->waiters--; in down_interruptible()
212 if (s->value > 0 && s->waiters) in up()
|
| H A D | vchi_bsd.h | 151 int waiters; member
|
| /netbsd-src/sys/external/bsd/drm2/dist/drm/amd/amdkfd/ |
| H A D | kfd_events.c | 657 static void free_waiters(uint32_t num_events, struct kfd_event_waiter *waiters) in free_waiters() argument
662 if (waiters[i].event) in free_waiters()
663 remove_wait_queue(&waiters[i].event->wq, in free_waiters()
664 &waiters[i].wait); in free_waiters()
666 kfree(waiters); in free_waiters()
|
| /netbsd-src/sys/arch/sparc/sparc/ |
| H A D | lock_stubs.s | 113 ldub [%o0 + MTX_LOCK], %o3 ! get has-waiters indicator
114 tst %o3 ! has waiters?
|
| /netbsd-src/external/bsd/openldap/dist/doc/guide/admin/ |
| H A D | monitoringslapd.sdf | 469 It contains the number of current read waiters.
473 Read waiters:
482 Write waiters:
|
| /netbsd-src/external/bsd/openldap/dist/servers/slapd/back-monitor/ |
| H A D | README | 231 It contains the number of current read waiters.
|
| /netbsd-src/sys/dev/dm/doc/ |
| H A D | locking.txt | 202 * Function release table lock and eventually wakeup all waiters.
|
| /netbsd-src/external/mpl/dhcp/dist/includes/ |
| H A D | dhcpd.h | 1497 caddr_t waiters; /* Pointer to list of things waiting member
|
| /netbsd-src/external/gpl3/gcc/dist/libstdc++-v3/ |
| H A D | ChangeLog | 2684 Use relaxed memory order and always notify all waiters.
|
| H A D | ChangeLog-2021 | 7118 * include/bits/atomic_wait.h: Always notify waiters in the
|
| /netbsd-src/games/fortune/datfiles/ |
| H A D | limerick-o.real | 6128 The waiters were all hanging low.
|
| /netbsd-src/external/gpl3/gcc/dist/libgcc/ |
| H A D | ChangeLog | 1032 (__gthread_cond_signal): Return early if no waiters. Consume
|
| /netbsd-src/external/gpl3/gcc/dist/libgomp/ |
| H A D | ChangeLog | 701 * config/nvptx/bar.h (gomp_barrier_t): Add fields waiters and lock.
|