| /src/external/gpl3/gcc.old/dist/libgomp/config/nvptx/ |
| bar.c | 69 unsigned int waiters local
70 = __atomic_add_fetch (&bar->waiters, 1, MEMMODEL_ACQ_REL);
71 if (waiters == 0)
73 unsigned int waiter_id = waiters;
75 if (waiters > 1)
78 asm volatile ("bar.sync 1, %0;" : : "r" (32 * waiters));
80 /* Ensure that they have updated waiters. */
81 asm volatile ("bar.sync 1, %0;" : : "r" (32 * waiters));
89 asm volatile ("bar.sync 1, %0;" : : "r" (32 * (waiters + 1)));
91 /* Get updated waiters. *
121 unsigned int waiters = __atomic_load_n (&bar->waiters, MEMMODEL_ACQUIRE); local
[all...] |
| bar.h | 41 unsigned waiters; member in struct:__anon16844
62 bar->waiters = 0;
|
| /src/sys/external/bsd/drm2/dist/drm/radeon/ |
| radeon_semaphore.c | 55 (*semaphore)->waiters = 0;
71 --semaphore->waiters;
88 ++semaphore->waiters;
104 if ((*semaphore)->waiters > 0) {
105 dev_err(rdev->dev, "semaphore %p has more waiters than signalers,"
|
| radeon_trace.h | 178 __field(signed, waiters)
184 __entry->waiters = sem->waiters;
188 TP_printk("ring=%u, waiters=%d, addr=%010Lx", __entry->ring,
189 __entry->waiters, __entry->gpu_addr)
|
| radeon.h | 619 signed waiters; member in struct:radeon_semaphore
|
| /src/external/bsd/ntp/dist/libntp/lib/isc/win32/include/isc/ |
| condition.h | 43 unsigned int waiters; member in struct:isc_condition
|
| /src/external/bsd/tmux/dist/ |
| cmd-wait-for.c | 54 TAILQ_HEAD(, wait_item) waiters;
94 TAILQ_INIT(&wc->waiters);
109 if (!TAILQ_EMPTY(&wc->waiters) || !wc->woken)
148 if (TAILQ_EMPTY(&wc->waiters) && !wc->woken) {
149 log_debug("signal wait channel %s, no waiters", wc->name);
153 log_debug("signal wait channel %s, with waiters", wc->name);
155 TAILQ_FOREACH_SAFE(wi, &wc->waiters, entry, wi1) {
158 TAILQ_REMOVE(&wc->waiters, wi, entry);
190 TAILQ_INSERT_TAIL(&wc->waiters, wi, entry);
250 TAILQ_FOREACH_SAFE(wi, &wc->waiters, entry, wi1)
[all...] |
| /src/external/lgpl2/userspace-rcu/dist/src/ |
| urcu-wait.h | 82 * Atomically move all waiters from wait queue into our local struct
86 void urcu_move_waiters(struct urcu_waiters *waiters,
89 waiters->head = __cds_wfs_pop_all(&queue->stack);
188 void urcu_wake_all_waiters(struct urcu_waiters *waiters)
192 /* Wake all waiters in our stack head */
193 cds_wfs_for_each_blocking_safe(waiters->head, iter, iter_n) {
|
| urcu-qsbr.c | 234 struct urcu_waiters waiters; local
268 * Move all waiters into our local queue.
270 urcu_move_waiters(&waiters, &gp_waiters);
335 urcu_wake_all_waiters(&waiters);
356 struct urcu_waiters waiters; local
387 * Move all waiters into our local queue.
389 urcu_move_waiters(&waiters, &gp_waiters);
430 urcu_wake_all_waiters(&waiters);
|
| urcu.c | 344 struct urcu_waiters waiters; local
368 * Move all waiters into our local queue.
370 urcu_move_waiters(&waiters, &gp_waiters);
453 * Wakeup waiters only after we have completed the grace period
457 urcu_wake_all_waiters(&waiters);
|
| /src/external/bsd/ntp/dist/libntp/lib/isc/win32/ |
| condition.c | 39 cond->waiters = 0;
178 REQUIRE(cond->waiters == 0);
203 * number of waiters > 0. Always reacquire the mutex regardless of the
220 cond->waiters++;
225 cond->waiters--;
|
| /src/sys/external/bsd/vchiq/dist/interface/compat/ |
| vchi_bsd.c | 157 s->waiters++;
159 s->waiters--;
173 s->waiters++;
175 s->waiters--;
212 if (s->value > 0 && s->waiters)
|
| vchi_bsd.h | 151 int waiters; member in struct:semaphore
|
| /src/lib/librumpuser/ |
| rumpfiber.c | 678 struct waithead waiters; member in struct:rumpuser_mtx
692 TAILQ_INIT(&mtx->waiters);
711 wait(&mtx->waiters, 0);
749 wakeup_one(&mtx->waiters);
757 assert(TAILQ_EMPTY(&mtx->waiters) && mtx->o == NULL);
905 struct waithead waiters; member in struct:rumpuser_cv
916 TAILQ_INIT(&cv->waiters);
958 wait(&cv->waiters, 0);
969 wait(&cv->waiters, 0);
983 rv = wait(&cv->waiters, sec * 1000 + nsec / (1000*1000))
[all...] |
| /src/sys/arch/sparc/sparc/ |
| lock_stubs.s | 96 * However, since we need to test the waiters condition, in the
100 * clear the lock and then test for waiters without worrying about
113 ldub [%o0 + MTX_LOCK], %o3 ! get has-waiters indicator
114 tst %o3 ! has waiters?
|
| /src/external/lgpl2/userspace-rcu/dist/tests/regression/ |
| rcutorture.h | 379 struct urcu_waiters waiters; local
381 urcu_move_waiters(&waiters, &call_rcu_waiters);
382 urcu_wake_all_waiters(&waiters);
|
| /src/sys/external/bsd/drm2/dist/drm/amd/amdkfd/ |
| kfd_events.c | 247 /* Wake up pending waiters. They will return failure */
578 * @event_waiters: Array of event waiters, one per event
657 static void free_waiters(uint32_t num_events, struct kfd_event_waiter *waiters)
662 if (waiters[i].event)
663 remove_wait_queue(&waiters[i].event->wq,
664 &waiters[i].wait);
666 kfree(waiters);
|
| /src/external/mpl/dhcp/dist/includes/ |
| dhcpd.h | 1497 caddr_t waiters; /* Pointer to list of things waiting member in struct:dns_query
|
