Home
last modified time | relevance | path

Searched refs:work (Results 1 – 25 of 1695) sorted by relevance

12345678910>>...68

/openbsd-src/sys/dev/pci/drm/include/linux/
H A Dworkqueue.h80 INIT_WORK(struct work_struct *work, work_func_t func) in INIT_WORK() argument
82 work->tq = NULL; in INIT_WORK()
83 task_set(&work->task, (void (*)(void *))func, work); in INIT_WORK()
89 queue_work(struct workqueue_struct *wq, struct work_struct *work) in queue_work() argument
91 work->tq = (struct taskq *)wq; in queue_work()
92 return task_add(work->tq, &work->task); in queue_work()
96 cancel_work(struct work_struct *work) in cancel_work() argument
98 if (work->tq != NULL) in cancel_work()
99 task_del(work->tq, &work->task); in cancel_work()
103 cancel_work_sync(struct work_struct *work) in cancel_work_sync() argument
[all …]
H A Dirq_work.h44 init_irq_work(struct irq_work *work, irq_work_func_t func) in init_irq_work() argument
46 work->tq = (struct taskq *)system_wq; in init_irq_work()
47 task_set(&work->task, (void (*)(void *))func, work); in init_irq_work()
51 irq_work_queue(struct irq_work *work) in irq_work_queue() argument
53 return task_add(work->tq, &work->task); in irq_work_queue()
57 irq_work_sync(struct irq_work *work) in irq_work_sync() argument
59 taskq_barrier(work->tq); in irq_work_sync()
/openbsd-src/sys/dev/pci/drm/
H A Ddrm_flip_work.c57 void drm_flip_work_queue_task(struct drm_flip_work *work, in drm_flip_work_queue_task() argument
62 spin_lock_irqsave(&work->lock, flags); in drm_flip_work_queue_task()
63 list_add_tail(&task->node, &work->queued); in drm_flip_work_queue_task()
64 spin_unlock_irqrestore(&work->lock, flags); in drm_flip_work_queue_task()
76 void drm_flip_work_queue(struct drm_flip_work *work, void *val) in drm_flip_work_queue() argument
83 drm_flip_work_queue_task(work, task); in drm_flip_work_queue()
85 DRM_ERROR("%s could not allocate task!\n", work->name); in drm_flip_work_queue()
86 work->func(work, val); in drm_flip_work_queue()
101 void drm_flip_work_commit(struct drm_flip_work *work, in drm_flip_work_commit() argument
106 spin_lock_irqsave(&work->lock, flags); in drm_flip_work_commit()
[all …]
H A Ddrm_vblank_work.c50 struct drm_vblank_work *work, *next; in drm_handle_vblank_works() local
56 list_for_each_entry_safe(work, next, &vblank->pending_work, node) { in drm_handle_vblank_works()
57 if (!drm_vblank_passed(count, work->count)) in drm_handle_vblank_works()
60 list_del_init(&work->node); in drm_handle_vblank_works()
62 kthread_queue_work(vblank->worker, &work->base); in drm_handle_vblank_works()
74 struct drm_vblank_work *work, *next; in drm_vblank_cancel_pending_works() local
78 list_for_each_entry_safe(work, next, &vblank->pending_work, node) { in drm_vblank_cancel_pending_works()
79 list_del_init(&work->node); in drm_vblank_cancel_pending_works()
108 int drm_vblank_work_schedule(struct drm_vblank_work *work, in drm_vblank_work_schedule() argument
111 struct drm_vblank_crtc *vblank = work->vblank; in drm_vblank_work_schedule()
[all …]
/openbsd-src/gnu/lib/libiberty/src/
H A Dcplus-dem.c61 #define CURRENT_DEMANGLING_STYLE work->options
144 #define PRINT_ANSI_QUALIFIERS (work -> options & DMGL_ANSI)
145 #define PRINT_ARG_TYPES (work -> options & DMGL_PARAMS)
322 #define SCOPE_STRING(work) ((work->options & DMGL_JAVA) ? "." : "::") argument
348 demangle_template_template_parm (struct work_stuff *work,
352 demangle_template (struct work_stuff *work, const char **, string *,
640 struct work_stuff work[1]; in cplus_demangle_opname() local
646 memset ((char *) work, 0, sizeof (work)); in cplus_demangle_opname()
647 work->options = options; in cplus_demangle_opname()
655 if (do_type (work, &tem, &type)) in cplus_demangle_opname()
[all …]
H A Dsort.c47 void sort_pointers (size_t n, void **pointers, void **work) in sort_pointers() argument
123 work[--count[((digit_t *) pointerp)[j]]] = *pointerp; in sort_pointers()
128 pointers = work; in sort_pointers()
129 work = pointerp; in sort_pointers()
151 void **work; in main() local
159 work = XNEWVEC (void*, k); in main()
167 sort_pointers (k, pointers, work); in main()
181 free (work); in main()
/openbsd-src/gnu/usr.bin/perl/cpan/Term-ReadKey/
H A DReadKey.xs781 struct tbuffer work; in ReadMode() local
792 if (!GetConsoleMode((HANDLE)_get_osfhandle(handle), &work.Mode)) in ReadMode()
800 tcgetattr(handle,&work); in ReadMode()
808 ioctl(handle,TCGETA,&work); in ReadMode()
815 ioctl(handle,TIOCGETP,&work.buf); in ReadMode()
817 ioctl(handle,TIOCGETC,&work.tchar); in ReadMode()
820 ioctl(handle,TIOCLGET,&work.local); in ReadMode()
823 ioctl(handle,TIOCGLTC,&work.ltchar); in ReadMode()
832 memcpy((void*)&savebuf,(void*)&work,sizeof(struct tbuffer)); in ReadMode()
854 …work.Mode &= ~(ENABLE_ECHO_INPUT|ENABLE_PROCESSED_INPUT|ENABLE_LINE_INPUT|ENABLE_PROCESSED_OUTPUT); in ReadMode()
[all …]
/openbsd-src/gnu/llvm/compiler-rt/lib/lsan/
H A Dlsan_mac.cpp138 void dispatch_async(dispatch_queue_t dq, void (^work)(void));
140 void (^work)(void));
142 void (^work)(void));
144 void (^work)(void));
146 void (^work)(void));
149 #define GET_LSAN_BLOCK(work) \ argument
154 work(); \
157 INTERCEPTOR(void, dispatch_async, dispatch_queue_t dq, void (^work)(void)) {
158 GET_LSAN_BLOCK(work);
163 dispatch_queue_t dq, void (^work)(void)) {
[all …]
/openbsd-src/gnu/usr.bin/gcc/gcc/config/arm/
H A Dlib1funcs.asm153 work .req r4 @ XXXX is this safe ? label
257 @ Load the constant 0x10000000 into our work register.
258 mov work, #1
259 lsl work, #28
265 cmp divisor, work
273 @ Set work to 0x80000000
274 lsl work, #3
278 cmp divisor, work
296 lsr work, divisor, #1
297 cmp dividend, work
[all …]
/openbsd-src/sys/dev/pci/drm/apple/
H A Dsystemep.c28 struct work_struct work; member
33 struct systemep_work *work = in system_log_work() local
34 container_of(work_, struct systemep_work, work); in system_log_work()
36 afk_send_command(work->service, SYSTEM_SET_PROPERTY, in system_log_work()
40 complete(&work->service->ep->dcp->systemep_done); in system_log_work()
41 kfree(work); in system_log_work()
47 struct systemep_work *work; in system_init() local
56 work = kzalloc(sizeof(*work), GFP_KERNEL); in system_init()
57 if (!work) in system_init()
60 work->service = service; in system_init()
[all …]
/openbsd-src/gnu/llvm/compiler-rt/lib/asan/
H A Dasan_mac.cpp236 void dispatch_async(dispatch_queue_t dq, void(^work)(void));
238 void(^work)(void));
240 void(^work)(void));
242 void(^work)(void));
243 void dispatch_source_set_event_handler(dispatch_source_t ds, void(^work)(void));
246 #define GET_ASAN_BLOCK(work) \ argument
252 work(); \
256 dispatch_queue_t dq, void(^work)(void)) {
258 GET_ASAN_BLOCK(work);
263 dispatch_group_t dg, dispatch_queue_t dq, void(^work)(void)) {
[all …]
/openbsd-src/gnu/usr.bin/binutils/gas/
H A Dflonum-mult.c82 unsigned long work; in flonum_multip() local
120 work = carry; in flonum_multip()
129 A, a->low[A], B, b->low[B], work); in flonum_multip()
135 work += (unsigned long) a->low[A] * (unsigned long) b->low[B]; in flonum_multip()
136 carry += work >> LITTLENUM_NUMBER_OF_BITS; in flonum_multip()
137 work &= LITTLENUM_MASK; in flonum_multip()
139 printf ("work=%08x carry=%04x\n", work, carry); in flonum_multip()
143 significant |= work; in flonum_multip()
148 product->low[P] = work; in flonum_multip()
150 printf ("P=%d. work[p]:=%04x\n", P, work); in flonum_multip()
[all …]
/openbsd-src/gnu/usr.bin/binutils-2.17/gas/
H A Dflonum-mult.c82 unsigned long work; in flonum_multip() local
120 work = carry; in flonum_multip()
129 A, a->low[A], B, b->low[B], work); in flonum_multip()
135 work += (unsigned long) a->low[A] * (unsigned long) b->low[B]; in flonum_multip()
136 carry += work >> LITTLENUM_NUMBER_OF_BITS; in flonum_multip()
137 work &= LITTLENUM_MASK; in flonum_multip()
139 printf ("work=%08x carry=%04x\n", work, carry); in flonum_multip()
143 significant |= work; in flonum_multip()
148 product->low[P] = work; in flonum_multip()
150 printf ("P=%d. work[p]:=%04x\n", P, work); in flonum_multip()
[all …]
/openbsd-src/distrib/miniroot/
H A Dlist2sh.awk79 work=$0;
80 gsub("[\\\\]", "\\\\", work);
81 gsub("[\"]", "\\\"", work);
82 gsub("[$]", "\\$", work);
83 gsub("[`]", "\\`", work);
84 printf("echo \"%s\"\n", work);
85 work=$0;
86 sub("^[ ]*" $1 "[ ]*", "", work);
87 printf("(cd ${TARGDIR}; %s)\n", work);
/openbsd-src/gnu/usr.bin/perl/t/bigmem/
H A Dindex.t21 my $work = $space x 0x80000002;
22 substr($work, 0x80000000) = "\n\n";
25 is(index($work, "\n"), 0x80000000, "test index() over 2G mark");
28 is(rindex($work, "\n"), 0x80000001, "test rindex() over 2G mark");
30 utf8::upgrade($work);
33 is(index($work, "\n"), 0x80000000, "test index() over 2G mark (utf8-ish)");
36 is(rindex($work, "\n"), 0x80000001, "test rindex() over 2G mark (utf8-ish)");
/openbsd-src/gnu/gcc/gcc/config/arm/
H A Dlib1funcs.asm325 work .req r4 @ XXXX is this safe ? label
548 @ Load the constant 0x10000000 into our work register.
549 mov work, #1
550 lsl work, #28
556 cmp divisor, work
564 @ Set work to 0x80000000
565 lsl work, #3
569 cmp divisor, work
587 lsr work, divisor, #1
588 cmp dividend, work
[all …]
/openbsd-src/gnu/gcc/libgomp/testsuite/libgomp.c/appendix-a/
H A Da.18.1.c11 int work[NUMBER_OF_THREADS]; variable
30 #pragma omp parallel private(iam,neighbor) shared(work,synch) in main()
36 work[iam] = fn1 (iam); in main()
41 #pragma omp flush(work,synch) in main()
54 #pragma omp flush(work,synch) in main()
56 result[iam] = fn2 (work[neighbor], work[iam]); in main()
/openbsd-src/gnu/usr.bin/gcc/gcc/testsuite/g77.f-torture/compile/
H A D20000511-2.f1 subroutine sgbcon(norm,n,kl,ku,ab,ldab,ipiv,anorm,rcond,work,iwork argument
16 real ab(ldab,n),work(n) local
51 t= work(jp)
54 work(jp)= work(j)
55 work(j)= t
58 call saxpy(lm,-t,ab(kd+1,j),1,work(j+1),1)
/openbsd-src/sys/dev/pci/drm/include/drm/
H A Ddrm_flip_work.h52 typedef void (*drm_flip_func_t)(struct drm_flip_work *work, void *val);
83 void drm_flip_work_queue_task(struct drm_flip_work *work,
85 void drm_flip_work_queue(struct drm_flip_work *work, void *val);
86 void drm_flip_work_commit(struct drm_flip_work *work,
88 void drm_flip_work_init(struct drm_flip_work *work,
90 void drm_flip_work_cleanup(struct drm_flip_work *work);
H A Ddrm_vblank_work.h64 int drm_vblank_work_schedule(struct drm_vblank_work *work,
66 void drm_vblank_work_init(struct drm_vblank_work *work, struct drm_crtc *crtc,
67 void (*func)(struct kthread_work *work));
68 bool drm_vblank_work_cancel_sync(struct drm_vblank_work *work);
69 void drm_vblank_work_flush(struct drm_vblank_work *work);
/openbsd-src/gnu/usr.bin/perl/t/run/
H A Dswitches.t229 local $TODO = ''; # these work on VMS
268 local $TODO = ''; # these ones should work on VMS
302 local $TODO = ''; # these ones should work on VMS
321 local $TODO = ''; # these ones should work on VMS
337 local $TODO = ''; # these ones should work on VMS
364 local $TODO = ''; # these ones should work on VMS
449 my $work = File::Spec->catfile($tmpinplace, "foo");
454 open my $fh, ">", $work or die "$0: failed to open '$work': $!";
461 args => [ $work ],
[all...]
/openbsd-src/sys/dev/pci/drm/amd/display/amdgpu_dm/
H A Damdgpu_dm_hdcp.c152 static void link_lock(struct hdcp_workqueue *work, bool lock) in link_lock() argument
156 for (i = 0; i < work->max_link; i++) { in link_lock()
158 mutex_lock(&work[i].mutex); in link_lock()
160 mutex_unlock(&work[i].mutex); in link_lock()
273 static void event_callback(struct work_struct *work) in event_callback() argument
277 hdcp_work = container_of(to_delayed_work(work), struct hdcp_workqueue, in event_callback()
292 static void event_property_update(struct work_struct *work) in event_property_update() argument
294 struct hdcp_workqueue *hdcp_work = container_of(work, struct hdcp_workqueue, in event_property_update()
363 static void event_property_validate(struct work_struct *work) in event_property_validate() argument
366 container_of(to_delayed_work(work), struct hdcp_workqueue, property_validate_dwork); in event_property_validate()
[all …]
/openbsd-src/sys/dev/pci/drm/amd/amdgpu/
H A Damdgpu_display.c51 * amdgpu_display_hotplug_work_func - work handler for display hotplug event
53 * @work: work struct pointer
55 * This is the hotplug event work handler (all ASICs).
56 * The work gets scheduled from the IRQ handler if there
62 * from the IRQ handler to a work handler because hotplug handler has to use
66 void amdgpu_display_hotplug_work_func(struct work_struct *work) in amdgpu_display_hotplug_work_func() argument
68 struct amdgpu_device *adev = container_of(work, struct amdgpu_device, in amdgpu_display_hotplug_work_func()
69 hotplug_work.work); in amdgpu_display_hotplug_work_func()
93 struct amdgpu_flip_work *work in amdgpu_display_flip_callback() local
100 amdgpu_display_flip_handle_fence(struct amdgpu_flip_work * work,struct dma_fence ** f) amdgpu_display_flip_handle_fence() argument
122 struct amdgpu_flip_work *work = amdgpu_display_flip_work_func() local
173 struct amdgpu_flip_work *work = amdgpu_display_unpin_work_func() local
200 struct amdgpu_flip_work *work; amdgpu_display_crtc_page_flip_target() local
[all...]
/openbsd-src/gnu/usr.bin/gcc/gcc/doc/
H A Dcontrib.texi57 Geoff Berry for his Java object serialization work and various patches.
68 garbage collector}, IA-64 libffi port, and other Java work.
71 Neil Booth for work on cpplib, lang hooks, debug hooks and other
91 Dave Brolley for work on cpplib and Chill.
115 Paolo Carlini for libstdc++ work: lots of efficiency improvements to
116 the string class, hard detective work on the frustrating localization
120 John Carr for his alias work, SPARC hacking, infrastructure improvements,
150 Nick Clifton for arm, mcore, fr30, v850, m32r work, @option{--help}, and
191 Ulrich Drepper for his work on glibc, testing of GCC using glibc, ISO C99
195 architecture, libio maintenance, and early math work.
[all …]
/openbsd-src/gnu/gcc/gcc/doc/
H A Dcontrib.texi42 Peter Barada for his work to improve code generation for new
65 Geoff Berry for his Java object serialization work and various patches.
83 garbage collector}, IA-64 libffi port, and other Java work.
86 Neil Booth for work on cpplib, lang hooks, debug hooks and other
110 Dave Brolley for work on cpplib and Chill.
113 Paul Brook for work on the ARM architecture and maintaining GNU Fortran.
137 Paolo Carlini for libstdc++ work: lots of efficiency improvements to
138 the C++ strings, streambufs and formatted I/O, hard detective work on
142 John Carr for his alias work, SPARC hacking, infrastructure improvements,
172 Nick Clifton for arm, mcore, fr30, v850, m32r work, @option{--help}, and
[all …]

12345678910>>...68