| /xsrc/external/mit/MesaLib/dist/src/egl/main/ |
| eglsync.h | 44 /* A sync is a display resource */
56 _eglInitSync(_EGLSync *sync, _EGLDisplay *disp, EGLenum type,
61 _eglGetSyncAttrib(_EGLDisplay *disp, _EGLSync *sync,
66 * Increment reference count for the sync.
69 _eglGetSync(_EGLSync *sync)
71 if (sync)
72 _eglGetResource(&sync->Resource);
73 return sync;
78 * Decrement reference count for the sync.
81 _eglPutSync(_EGLSync *sync)
116 _EGLSync *sync = (_EGLSync *) handle; local
[all...] |
| eglsync.c | 39 * Parse the list of sync attributes and return the proper error code.
42 _eglParseSyncAttribList(_EGLSync *sync, const EGLAttrib *attrib_list)
56 if (sync->Type == EGL_SYNC_CL_EVENT_KHR) {
57 sync->CLEvent = val;
63 if (sync->Type == EGL_SYNC_NATIVE_FENCE_ANDROID) {
65 sync->SyncFd = val;
76 _eglLog(_EGL_DEBUG, "bad sync attribute 0x%" PRIxPTR, attr);
86 _eglInitSync(_EGLSync *sync, _EGLDisplay *disp, EGLenum type,
91 _eglInitResource(&sync->Resource, sizeof(*sync), disp)
[all...] |
| /xsrc/external/mit/MesaLib.old/dist/src/egl/main/ |
| eglsync.h | 44 /* A sync is a display resource */
56 _eglInitSync(_EGLSync *sync, _EGLDisplay *disp, EGLenum type,
61 _eglGetSyncAttrib(_EGLDriver *drv, _EGLDisplay *disp, _EGLSync *sync,
66 * Increment reference count for the sync.
69 _eglGetSync(_EGLSync *sync)
71 if (sync)
72 _eglGetResource(&sync->Resource);
73 return sync;
78 * Decrement reference count for the sync.
81 _eglPutSync(_EGLSync *sync)
116 _EGLSync *sync = (_EGLSync *) handle; local
[all...] |
| eglsync.c | 39 * Parse the list of sync attributes and return the proper error code.
42 _eglParseSyncAttribList(_EGLSync *sync, const EGLAttrib *attrib_list)
56 if (sync->Type == EGL_SYNC_CL_EVENT_KHR) {
57 sync->CLEvent = val;
63 if (sync->Type == EGL_SYNC_NATIVE_FENCE_ANDROID) {
65 sync->SyncFd = val;
76 _eglLog(_EGL_DEBUG, "bad sync attribute 0x%" PRIxPTR, attr);
86 _eglInitSync(_EGLSync *sync, _EGLDisplay *disp, EGLenum type,
91 _eglInitResource(&sync->Resource, sizeof(*sync), disp)
[all...] |
| /xsrc/external/mit/MesaLib/dist/src/mesa/main/ |
| syncobj.h | 26 * Sync object management.
51 _mesa_get_and_ref_sync(struct gl_context *ctx, GLsync sync, bool incRefCount);
58 _mesa_IsSync(GLsync sync);
61 _mesa_DeleteSync_no_error(GLsync sync);
64 _mesa_DeleteSync(GLsync sync);
73 _mesa_ClientWaitSync_no_error(GLsync sync, GLbitfield flags, GLuint64 timeout);
76 _mesa_ClientWaitSync(GLsync sync, GLbitfield flags, GLuint64 timeout);
79 _mesa_WaitSync_no_error(GLsync sync, GLbitfield flags, GLuint64 timeout);
82 _mesa_WaitSync(GLsync sync, GLbitfield flags, GLuint64 timeout);
85 _mesa_GetSynciv(GLsync sync, GLenum pname, GLsizei bufSize, GLsizei *length
[all...] |
| syncobj.c | 26 * Sync object management.
28 * Unlike textures and other objects that are shared between contexts, sync
30 * and delete behavior of sync objects is slightly different. References to
31 * sync objects are added:
45 * As with shader objects, sync object names become invalid as soon as
109 * whether the state of the sync object has changed.
124 * the state of the sync object changes or the timeout expires.
144 * Allocate/init the context state related to sync objects.
154 * Free the context state related to sync objects.
164 * Check if the given sync object is
[all...] |
| /xsrc/external/mit/MesaLib.old/dist/src/mesa/main/ |
| syncobj.h | 26 * Sync object management.
51 _mesa_get_and_ref_sync(struct gl_context *ctx, GLsync sync, bool incRefCount);
58 _mesa_IsSync(GLsync sync);
61 _mesa_DeleteSync_no_error(GLsync sync);
64 _mesa_DeleteSync(GLsync sync);
73 _mesa_ClientWaitSync_no_error(GLsync sync, GLbitfield flags, GLuint64 timeout);
76 _mesa_ClientWaitSync(GLsync sync, GLbitfield flags, GLuint64 timeout);
79 _mesa_WaitSync_no_error(GLsync sync, GLbitfield flags, GLuint64 timeout);
82 _mesa_WaitSync(GLsync sync, GLbitfield flags, GLuint64 timeout);
85 _mesa_GetSynciv(GLsync sync, GLenum pname, GLsizei bufSize, GLsizei *length
[all...] |
| syncobj.c | 26 * Sync object management.
28 * Unlike textures and other objects that are shared between contexts, sync
30 * and delete behavior of sync objects is slightly different. References to
31 * sync objects are added:
45 * As with shader objects, sync object names become invalid as soon as
108 * whether the state of the sync object has changed.
123 * the state of the sync object changes or the timeout expires.
143 * Allocate/init the context state related to sync objects.
153 * Free the context state related to sync objects.
163 * Check if the given sync object is
[all...] |
| /xsrc/external/mit/MesaLib/dist/src/android_stub/ |
| sync_stub.cpp | 2 #include <sync/sync.h>
|
| /xsrc/external/mit/xf86-video-nouveau/dist/src/ |
| nouveau_sync.c | 43 pNv->sync; \
67 SyncScreenFuncsPtr sync = miSyncGetScreenFuncs(screen); local
70 swap(priv, sync, CreateFence);
71 sync->CreateFence(screen, fence, triggered);
72 swap(priv, sync, CreateFence);
81 SyncScreenFuncsPtr sync = miSyncGetScreenFuncs(screen); local
85 unwrap(priv, sync, CreateFence);
87 pNv->sync = NULL;
97 SyncScreenFuncsPtr sync; local
99 priv = pNv->sync = calloc(1, sizeof(*priv))
[all...] |
| /xsrc/external/mit/MesaLib/dist/src/mesa/drivers/dri/i915/ |
| intel_syncobj.c | 35 * application is using many sync objects, it will emit small batchbuffers
154 * so given that the sync object has already flushed the batchbuffer, any
163 struct intel_gl_sync_object *sync; local
165 sync = calloc(1, sizeof(*sync));
166 if (!sync)
169 return &sync->Base;
175 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
177 intel_fence_finish(&sync->fence);
178 free(sync);
186 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
196 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
207 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
215 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
[all...] |
| /xsrc/external/mit/MesaLib.old/dist/src/mesa/drivers/dri/i915/ |
| intel_syncobj.c | 35 * application is using many sync objects, it will emit small batchbuffers
156 * so given that the sync object has already flushed the batchbuffer, any
165 struct intel_gl_sync_object *sync; local
167 sync = calloc(1, sizeof(*sync));
168 if (!sync)
171 return &sync->Base;
177 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
179 intel_fence_finish(&sync->fence);
180 free(sync);
188 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
198 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
209 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
217 struct intel_gl_sync_object *sync = (struct intel_gl_sync_object *)s; local
[all...] |
| /xsrc/external/mit/MesaLib.old/dist/src/mesa/drivers/dri/i965/ |
| brw_sync.c | 35 * application is using many sync objects, it will emit small batchbuffers
119 * When the condition of the sync object is satisfied by the fence
120 * command, the sync is signaled by the associated client API context,
122 * <sync> to unblock. The only condition currently supported is
124 * completion of the fence command corresponding to the sync object,
126 * command stream. The sync object will not be signaled until all
321 * so given that the sync object has already flushed the batchbuffer, any
342 struct brw_gl_sync *sync; local
344 sync = calloc(1, sizeof(*sync));
354 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
365 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
384 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
395 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
403 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
[all...] |
| /xsrc/external/mit/xorg-server/dist/miext/sync/ |
| misync.c | 34 /* Default implementations of the sync screen functions */
86 /* Machine independent portion of the fence sync object implementation */
105 pFence->sync.initialized = TRUE;
111 pFence->sync.beingDestroyed = TRUE;
113 if (pFence->sync.initialized) {
122 nt_list_for_each_entry_safe(ptl, pNext, pFence->sync.pTriglist, next) {
123 pFence->sync.pTriglist = pNext;
146 for (ptl = pFence->sync.pTriglist; ptl; ptl = ptl->next) {
|
| misyncstr.h | 37 /* Sync object types */
51 SyncObject sync; /* Common sync object data */ member in struct:_SyncCounter
57 SyncObject sync; /* Common sync object data */ member in struct:_SyncFence
88 /* Wrappable sync-specific screen functions */
|
| /xsrc/external/mit/xorg-server.old/dist/miext/sync/ |
| misyncstr.h | 36 /* Sync object types */
49 SyncObject sync; /* Common sync object data */ member in struct:_SyncCounter
55 SyncObject sync; /* Common sync object data */ member in struct:_SyncFence
|
| /xsrc/external/mit/MesaLib/dist/src/panfrost/vulkan/ |
| panvk_sync.c | 34 struct panvk_syncobj *sync,
47 sync->permanent = create.handle;
53 sync_set_temporary(struct panvk_device *device, struct panvk_syncobj *sync,
58 if (sync->temporary) {
59 struct drm_syncobj_destroy destroy = { .handle = sync->temporary };
63 sync->temporary = syncobj;
67 sync_destroy(struct panvk_device *device, struct panvk_syncobj *sync)
71 if (!sync)
74 sync_set_temporary(device, sync, 0);
75 struct drm_syncobj_destroy destroy = { .handle = sync->permanent }
[all...] |
| /xsrc/external/mit/MesaLib/dist/src/mesa/drivers/dri/i965/ |
| brw_sync.c | 35 * application is using many sync objects, it will emit small batchbuffers
206 * When the condition of the sync object is satisfied by the fence
207 * command, the sync is signaled by the associated client API context,
209 * <sync> to unblock. The only condition currently supported is
211 * completion of the fence command corresponding to the sync object,
213 * command stream. The sync object will not be signaled until all
408 * so given that the sync object has already flushed the batchbuffer, any
429 struct brw_gl_sync *sync; local
431 sync = calloc(1, sizeof(*sync));
441 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
453 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
472 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
483 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
491 struct brw_gl_sync *sync = (struct brw_gl_sync *) _sync; local
[all...] |
| /xsrc/external/mit/MesaLib/dist/src/virtio/vulkan/ |
| vn_renderer.h | 29 * A sync consists of a uint64_t counter. The counter can be updated by CPU
71 * Submit cs to the virtual sync queue identified by sync_queue_index. The
74 * VkQueue, the virtual sync queue is signaled.
80 * When sync_queue_cpu is true, it specifies the special CPU sync queue,
87 /* syncs to update when the virtual sync queue is signaled */
192 struct vn_renderer_sync *sync);
195 struct vn_renderer_sync *sync,
200 struct vn_renderer_sync *sync,
205 struct vn_renderer_sync *sync,
210 struct vn_renderer_sync *sync,
473 struct vn_renderer_sync *sync; local
[all...] |
| /xsrc/external/mit/MesaLib/dist/src/freedreno/vulkan/ |
| tu_kgsl.c | 314 TU_FROM_HANDLE(tu_syncobj, sync, syncobjs[i]);
317 if (!sync->timestamp_valid)
321 ret.timestamp = sync->timestamp;
323 ret.timestamp = max_ts(ret.timestamp, sync->timestamp);
325 ret.timestamp = min_ts(ret.timestamp, sync->timestamp);
329 sync->timestamp_valid = false;
415 struct kgsl_command_syncpoint sync = { local
427 .synclist = (uintptr_t) &sync,
451 "Failed to create sync file for timestamp: %s\n",
481 struct tu_syncobj *sync local
[all...] |
| tu_drm.c | 578 struct tu_syncobj *sync = local
579 vk_object_alloc(&device->vk, pAllocator, sizeof(*sync),
581 if (!sync)
591 vk_free2(&device->vk.alloc, pAllocator, sync);
595 sync->binary.permanent = create.handle;
596 sync->binary.temporary = 0;
597 sync->type = TU_SEMAPHORE_BINARY;
599 sync->type = TU_SEMAPHORE_TIMELINE;
600 sync->timeline.highest_signaled = sync->timeline.highest_submitted
[all...] |
| /xsrc/external/mit/MesaLib/dist/include/CL/ |
| cl_egl.h | 118 CLeglSyncKHR sync,
124 CLeglSyncKHR sync,
|
| /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/r600/sfn/ |
| sfn_debug.cpp | 37 int sync();
47 int stderr_streambuf::sync() function in class:r600::stderr_streambuf
|
| /xsrc/external/mit/MesaLib.old/dist/include/CL/ |
| cl_egl.h | 118 CLeglSyncKHR sync,
124 CLeglSyncKHR sync,
|
| /xsrc/external/mit/MesaLib/dist/src/amd/compiler/ |
| aco_scheduler.cpp | 443 memory_sync_info sync = get_sync_info(instr);
446 sync.storage = (storage_class)(sync.storage | storage_buffer);
447 sync.semantics =
448 (memory_semantics)((sync.semantics | semantic_private) & ~semantic_can_reorder);
450 return sync;
487 add_memory_event(memory_event_set* set, Instruction* instr, memory_sync_info* sync)
492 if (bar.sync.semantics & semantic_acquire)
493 set->bar_acquire |= bar.sync.storage;
494 if (bar.sync.semantics & semantic_release
[all...] |
