_init _fini _ITM_deregisterTMCloneTable _ITM_registerTMCloneTable __cxa_finalize __deregister_frame_info __register_frame_info fprintf gcoSURF_ConstructWrapper gcoSURF_SetOrientation gcoSURF_SetBuffer gcoSURF_SetWindow gcoSURF_Lock gcoSURF_SetColorType gcoSURF_SetVideoBuffer gcoSURF_Unlock gcoSURF_Destroy __stack_chk_fail __stack_chk_guard stderr g2d_open calloc gcoOS_Construct gcoHAL_Construct gcoOS_DeviceControl gcoHAL_GetHardwareType gcoHAL_SetHardwareType gcoOS_GetBaseAddress gcoHAL_IsFeatureAvailable gcoHAL_Get2DEngine gcoOS_GetEnv gcoOS_StrCmp isOCLEnabled gcoHAL_Destroy gcoOS_Destroy gcoHAL_IsFeatureAvailable1 g2d_init_opencl gcoHAL_GetVGEngine g2d_make_current g2d_clear gcoVG_SetTarget gcoVG_EnableMask gcoVG_SetImageMode gcoVG_SetBlendMode gcoVG_EnableScissor gcoVG_EnableColorTransform gcoVG_SetSolidPaint gcoVG_Clear gco2D_DisableAlphaBlend gco2D_SetPixelMultiplyModeAdvanced gco2D_SetTarget gco2D_SetClipping gco2D_Clear g2d_query_hardware g2d_query_feature g2d_query_cap g2d_enable gco2D_EnableDither gcoVG_EnableDither g2d_disable g2d_set_clipping g2d_blitEx gcoVG_DrawImageFilter gcoVG_SetColorTransform gco2D_SetCurrentSourceIndex gco2D_EnableAlphaBlendAdvanced gco2D_SetSourceGlobalColorAdvanced gco2D_SetTargetGlobalColorAdvanced gco2D_SetBitBlitMirror gcoHAL_QueryChipIdentity gco2D_SetSourceTileStatus gco2D_SetKernelSize gco2D_SetFilterType gco2D_SetStateU32 gco2D_FilterBlitEx2 gco2D_SetYUVColorMode gco2D_SetGenericTarget gco2D_LoadSolidBrush gco2D_Blit gco2D_SetGenericSource gco2D_SetSource gco2D_CalcStretchFactor gco2D_SetStretchFactors gco2D_StretchBlit g2d_opencl_conversion g2d_blit g2d_multi_blit gco2D_SetROP gco2D_MultiSourceBlit g2d_copy memcpy g2d_flush gcoHAL_Commit gcoHAL_Flush g2d_finish g2d_sync_opencl g2d_close g2d_close_opencl g2d_cache_op gcoOS_CacheClean gcoOS_CacheInvalidate gcoOS_CacheFlush g2d_alloc gcoOS_AllocateVideoMemory malloc g2d_free gcoOS_FreeVideoMemory g2d_buf_export_fd gcoHAL_ExportVideoMemory g2d_create_fence_fd gcoOS_CreateSignal gcoOS_CreateNativeFence gcoOS_GetCurrentProcessID gcoHAL_ScheduleEvent gcoOS_DestroySignal _G2D_VERSION getSystemEnvInt getenv strtol __errno_location g2d_buf_from_virt_addr g2d_buf_from_fd ioctl strerror clCreateBuffer clSetKernelArg clEnqueueNDRangeKernel clFlush clReleaseMemObject clFinish clReleaseKernel clReleaseProgram clReleaseCommandQueue clReleaseContext clGetPlatformIDs clGetDeviceIDs clCreateContext clCreateCommandQueue strlen clCreateProgramWithSource clBuildProgram clCreateKernel clGetProgramBuildInfo g_tile2linear_kernel libOpenCL.so.1 libGAL.so libc.so libg2d.so.2 OPENCL_1.0
: = = = $ = 2 = = = = = = # = = & = = = = = %s: surface format %d is not support by hardware vg ! %s: Invalid handle ! %s: 2D/VG PIPE not found! G2D_YUV_COLOR_MODE BT709 %s: fail with status %d %s: fail to set current hardware type to %d %s: Invalid area parameter! %s: Invalid clear rect, left %d, top %d, right %d, bottom %d! %s: surface format %d is not supported ! %s: Invalid src and dst parameters! %s: Invalid src rect, left %d, top %d, right %d, bottom %d, width %d, height %d, stride %d! %s: Invalid src planes[0] pointer=0x%llx ! %s: blend dim is only supported by gpu 2d ! %s: Invalid dst rect, left %d, top %d, right %d, bottom %d, width %d, height %d, stride %d! %s: Invalid dst planes[0] address=0x%llx ! %s: Invalid src format %d! %s: Invalid src format %d for dst format %d! %s, line%d: Invalid dst format %d! %s: G2D_PRE_MULTIPLIED_ALPHA should not be set with G2D_SRC_ALPHA, ignored %s: G2D_PRE_MULTIPLIED_ALPHA should not be set with G2D_DST_ALPHA, ignored %s: rotation is not supported by hardware vg, should enable G2D_HARDWARE_2D type %s: blend mode(0x%x, 0x%x) is not supported by hardware vg, should enable hardware 2d. %s: invalid color format for dim blit ! %s: invalid buffer ! %s: invalid buffer data! %s: fail with status %d %s: alloc memory fail with size %d! %s: malloc g2d_buf fail ! %s: malloc g2d_buf_context fail ! %s: invalid g2d_buf ! %s: g2d_free fail ! export this buf fail! %d %s: invalid handle ! %s: g2d_create_fence_fd fail ! g2d_construct_vg_surface g2d_open g2d_make_current g2d_clear g2d_clear_2d g2d_clear_vg g2d_query_hardware g2d_query_feature g2d_query_cap g2d_enable g2d_disable g2d_set_clipping g2d_blitEx g2d_blit_2d g2d_blit_vg g2d_multi_blit ?  g2d_multi_blit_2d g2d_flush g2d_finish g2d_close g2d_cache_op g2d_alloc g2d_free g2d_create_fence_fd $VERSION$6.4.3:398061:a80c529$ G2D_OCL_ENABLE %s: NOT SUPPORTED %s: ioctl DMA_BUF_IOCTL_PHYS failed: %s %s: get phys address failed %s: calloc g2d_buf failed g2d_buf_from_virt_addr g2d_ion_phys_dma g2d_buf_from_fd %s invalid opencl context line:%d %s Failed to Allocate memSrcY buffer %s Failed to Allocate memSrcUV buffer %s Failed to Allocate DstY buffer %s Failed to Allocate DstU buffer %s Failed to Allocate DstV buffer %s clSetKernelArg fail %d %s clEnqueueNDRangeKernel fail %d %s NDRangeKernel fail %d, offset2d[]= %zd, %zd, global2d[]= %zd, %zd, local2d[]=%zd %zd %s Failed to allocate opencl context %s Failed to initialize OpenCL %s error %d createProgramWithSource failed %8s %s Failed error %d %8s %s Failed to build kernel read_row_of_tiles %s failed to create %s: %d %s Failed to create kernel_read_row convert_10_to_8_bits %s Failed to create kernel_10_to_8 convert_yuyv_to_nv12 %s Failed to create kernel_yuyv_to_nv12 convert_yuyv_to_nv21 %s Failed to create kernel_yuyv_to_nv21 convert_nv12_to_yuv420 %s Failed to create kernel_nv12_to_yuv420 convert_yuyv_to_yuv420 %s Failed to create kernel_yuyv_to_yuv420 g2d_opencl_conversion g2d_sync_opencl g2d_close_opencl g2d_init_opencl BuildProgram CreateKernel : = = = $ = 2 = = = = = = # = = & = = = = =
0l #pragma unroll __kernel void convert_10_to_8_bits (__global unsigned char *buf_base, __global unsigned char *pbuffer, int nPicWidth, int stride, int vtile) { int x = get_global_id(0); int y = get_global_id(1); int dy = vtile*128; int sy = dy + y; { int sx = x * 5; uchar *outbuf = pbuffer + sy * nPicWidth + x * 4; uchar *pbuf = buf_base + (sy >> 7) * stride + ((sy & 127) << 3) + ((sx >> 3) << 10); int j_in_src = sx & 7; uchar8 input_bytes = vload8(0, pbuf + j_in_src); if (j_in_src > 3) { uchar4 temp_bytes = vload4(0, pbuf + 1024); vstore3(input_bytes.s123, 0, outbuf); vstore4(temp_bytes, 0, outbuf+7-j_in_src); input_bytes.s1234 = vload4(0, outbuf); } uint4 shift = {0,10,20,30}; unsigned int bit_pos = x * 40; shift = (shift + bit_pos) & 7; uchar4 output_bytes = input_bytes.s0123 << shift; uint4 temp_output = convert_uint4(input_bytes.s1234); output_bytes |= convert_uchar4(temp_output >> (8 - shift)); vstore4(output_bytes, 0, outbuf); } } __kernel void read_row_of_tiles (__global unsigned char *buf_base, __global unsigned char *pbuffer, int nPicWidth, int stride, int vtile) { int x = get_global_id(0); int y = get_global_id(1); int sy = vtile*128 + y; { int base_offset = (sy >> 7) * stride + x * 1024 + (sy & 127) * 8; int buf_offset = (sy * nPicWidth) + (x * 8); uchar8 bytes = vload8(0, buf_base + base_offset); vstore8(bytes, 0, pbuffer + buf_offset); } } __kernel void convert_yuyv_to_nv12 (__global unsigned char *buf_base, __global unsigned char *buf_luma, __global unsigned char *buf_chroma, int nPicWidth, int stride, int vtile) { int x = get_global_id(0); int y = get_global_id(1); int sy = vtile*128 + y; { uchar *pbuf = buf_base + x * 16 + stride * sy; uchar16 yuyv = vload16(0, pbuf); uchar8 y8 = yuyv.s02468ace; vstore8(y8, 0, buf_luma + x * 8 + nPicWidth * sy); if (sy & 1) { uchar8 uv8 = yuyv.s13579bdf; yuyv = vload16(0, pbuf - stride); uv8 = convert_uchar8((convert_ushort8(uv8) + convert_ushort8(yuyv.s13579bdf)) >> 1); vstore8(uv8, 0, buf_chroma + x * 8 + nPicWidth * (sy >> 1)); } } } __kernel void convert_yuyv_to_nv21 (__global unsigned char *buf_base, __global unsigned char *buf_luma, __global unsigned char *buf_chroma, int nPicWidth, int stride, int vtile) { int x = get_global_id(0); int y = get_global_id(1); int sy = vtile*128 + y; { uchar *pbuf = buf_base + x * 16 + stride * sy; uchar16 yuyv = vload16(0, pbuf); uchar8 y8 = yuyv.s02468ace; vstore8(y8, 0, buf_luma + x * 8 + nPicWidth * sy); if (sy & 1) { uchar8 uv8 = yuyv.s3175b9fd; yuyv = vload16(0, pbuf - stride); uv8 = convert_uchar8((convert_ushort8(uv8) + convert_ushort8(yuyv.s3175b9fd)) >> 1); vstore8(uv8, 0, buf_chroma + x * 8 + nPicWidth * (sy >> 1)); } } } __kernel void convert_nv12_to_yuv420 (__global uchar *srcY, __global uchar *srcUV, __global uchar *dstY, __global uchar *dstU, __global uchar *dstV, int srcStride, int dstStride, int leftover) { int x = get_global_id(0); int y = get_global_id(1); uchar16 y16 = vload16(x, srcY + 2 * y * srcStride + leftover); vstore16(y16, x, dstY + 2 * y * dstStride + leftover); uchar16 y16_line2 = vload16(x, srcY + (2 * y + 1) * srcStride + leftover); vstore16(y16_line2, x, dstY + (2 * y + 1)* dstStride + leftover); uchar16 uv16 = vload16(x, srcUV + y * srcStride + leftover); vstore8(uv16.s02468ace, x, dstU + y * dstStride / 2 + leftover / 2); vstore8(uv16.s13579bdf, x, dstV + y * dstStride / 2 + leftover / 2); } __kernel void convert_yuyv_to_yuv420 (__global uchar *srcY, __global uchar *srcUV, __global uchar *dstY, __global uchar *dstU, __global uchar *dstV, int srcStride, int dstStride, int leftover) { int x = get_global_id(0); int y = get_global_id(1); uchar16 yuyv0 = vload16(x, srcY + 2 * y * srcStride + leftover); vstore8(yuyv0.s02468ace, x, dstY + 2* y * dstStride + leftover); uchar16 yuyv1 = vload16(x, srcY + (2*y + 1) * srcStride + leftover); vstore8(yuyv1.s02468ace, x, dstY +(2*y + 1) * dstStride + leftover); uchar4 u4 = convert_uchar4((convert_ushort4(yuyv0.s159d) + convert_ushort4(yuyv1.s159d)) >> 1); uchar4 v4 = convert_uchar4((convert_ushort4(yuyv0.s37bf) + convert_ushort4(yuyv1.s37bf)) >> 1); vstore4(u4, x, dstU + y * dstStride / 2 + leftover / 2); vstore4(v4, x, dstV + y * dstStride / 2 + leftover / 2); }
GCC: (Buildroot 2022.02.1-17-g91dc2ea) 10.3.0
gcvSURF_ASTC5x4_SRGB gcvSECURE_IN_NORMAL long long int gcvFEATURE_INCORRECT_WR_REQ_TO_USC_BETWEEN_REORDER_AND_NORMAL_LAYER_FIX _gcsHAL_TIMESTAMP gcvSURF_ASTC10x10 chipModel gcvTLS_KEY_EGL gcvSURF_R5G6B5 gcoOS_StrCmp gcvSURF_BLEND_INVERSED_NO_CROSS gcvFEATURE_PA_LINECLIP_FIX gcvSURF_A32B32G32R32F_2_G32R32F gcvFEATURE_TX_VKBORDER_MODE gcvPOWER_OFF gcvFEATURE_USC gcvFEATURE_OCCLUSION_QUERY gcvSURF_PROTECTED_CONTENT externalMemoryInfo gcoSURF_ConstructWrapper gcvFEATURE_MIN_AREA gcvFEATURE_SHADER_HAS_W gcvFEATURE_S8_ONLY_RENDERING gcvSURF_Q8W8V8U8 allowFastClear gcvFEATURE_FORMAT_10BIT_CROSS_4K gcvSURF_A12 gcvSURF_A16 gcvSTATUS_INVALID_MIPMAP gcvSURF_B5G5R5A1 gcvFEATURE_NN_PRELU gcvVG_BLEND_ADDITIVE patchHead gcvSURF_X32B32G32R32F_4_A8R8G8B8 gcv2D_TSC_DEC_TPC_TILED_COMPRESSED gcvSURF_A32B32G32R32 srcRect gcvENGINE_INVALID gcvFEATURE_NN_DW_1x1_CONV_MERGE gcvFEATURE_OCB_REMAP_PHYSICAL_ADDRESS gcvFEATURE_NN_ZXDP3_KERNEL_READ_CONFLICT_FIX gcvFEATURE_BRANCH_ON_IMMEDIATE_REG G2D_RGB888 gcFEATURE_BIT_NN_IN_TILE_DATA_IS_ALL_PAD_FIX gcvFEATURE_NN_COMMAND_KERNEL_REQUEST_CONFICT_FIX gcvSURF_GLOBAL_ALPHA_ON gcvSURF_RENDER_TARGET_TS_DIRTY gcvSURF_B8G8R8UI gcvSURF_0_DEGREE srcFactorMode _gcsHAL_COMMAND_LOCATION gcvFEATURE_SH_IMAGE_LD_LAST_PIXEL_FIX gctCHAR gcFEATURE_NN_WASTE_COEF_READ_WRITE_BANDWIDTH_128BYTE_VIPSRAM_IN_FULL_PATIAL_CACHE_MODE_FIX gcvFEATURE_NN_ASYNC_COPY_MERGE_FIX gcvHAL_NAME_VIDEO_MEMORY gcvFEATURE_DIVISOR_STREAM_ADDR_FIX gcvSURF_A32 gcvSECURE_IN_TA gcvPOWER_FLAG_BROADCAST gcvSURF_BITMAP gcvSURF_B2G3R3UI gcvSTATUS_UNSAT_LIB_SYMBOL uintptr_t gcvFEATURE_TEXTURE_16K gcvTILING_SPLIT_BUFFER FreeNonPagedMemory gcvSURF_A4L12 gcvFEATURE_NON_POWER_OF_TWO G2D_BLUR g2d_blitEx reservedTail internalSize uscAttribCacheRatio g2d_flush hKernel gcvHAL_QUERY_CHIP_OPTION _gcsHAL_WAIT_FENCE major gcvFEATURE_DEPTHWISE_NEIGHBOR_IMG_DATA_TRANSFER_NOT_EFFICIENT_FIX gcv2D_STATE_DE_GAMMA gcvCORE_MAJOR gcvSUPERTILED_128B gcvSURF_UYVY gcvSURF_RENDER_TARGET_NO_COMPRESSION gcvSURF_L12 gcvSURF_L16 gcvSURF_ASTC8x6 enableNNTPParallel gcvSURF_ASTC8x8 G2D_UYVY gcv2D_STATE_ARRAY_YUV_SRC_TILE_STATUS_ADDR _gcsHAL_BOTTOM_HALF_UNLOCK_VIDEO_MEMORY gcvSTATUS_OUTPUT_ARRAY_SIZE_MISMATCH gcvFEATURE_SEPARATE_RT_CTRL compressed G2D_LINEAR gcvSURF_X16B16G16R16I_1_G32R32F gcvSURF_B8G8R8UI_1_A8R8G8B8 G2D_RGBA5551 gcvHARDWARE_2D gcvFEATURE_NO_NARROW_POST_PROCESS_PIPE gcv2D_TSC_TPC_COMPRESSED_V10 gcvSURF_B8G8R8X8 gcvSURF_NO_HZ gcvSURF_R8G8B8_1_A8R8G8B8 gcvSTATUS_GLOBAL_TYPE_MISMATCH gcvORIENTATION_BOTTOM_TOP gcvFILTER_POINT gcvFEATURE_VIP_HW_FINAL_RELEASE gcvCOMPRESSION_OPTION_COLOR gcvFEATURE_TEXTURE_LINEAR gcoOS_Construct gcvFEATURE_MSAA_OQ_FIX gcvSURF_R8G8B8X8 gcvSTATUS_TOO_MANY_INSTRUCTION gcoVG_SetImageMode gcvSURF_R3G3B2 request gcv2D_YUV_709 gcvHARDWARE_3D dstHeight gcv2D_TSC_TPC_COMPRESSED gcvHAL_READ_REGISTER_EX gcvTEXTURE_SWIZZLE_INVALID gcvHAL_GET_FRAME_INFO g2d_set_clipping gcvFEATURE_EVIS_NO_CORDIAC gcvSTATUS_COMPILER_FE_PREPROCESSOR_ERROR gcFEATURE_PREPROCESS_IMG_BUF_640BYTE_LIMIT gcvFEATURE_SHADER_HAS_SIGN gcvSURF_L32 gcvSURF_V8U8_1_A4R4G4B4 gcvSURF_NV12 gcvHAL_DEBUG_DUMP gcvSURF_NV16 gcvSURF_V16U16_1_A8R8G8B8 gcvSURF_A32B32G32R32I_4_A8R8G8B8 baseAddressVG G2D_BGR565 _gceSURF_COLOR_TYPE gcvFEATURE_TP_RTNE gcvSURF_A8B8G8R8I gcvSTATUS_FALSE gcvFEATURE_DEC300_COMPRESSION dstBits gcv5200 gcvFEATURE_SH_INSTRUCTION_PREFETCH gcvFEATURE_PE_MULTI_RT_BLEND_ENABLE_CONTROL g2d_buf has2DPipe gcvHAL_COMMIT next gcvSURF_NV21 gcvFEATURE_TX_FRAC_PRECISION_6BIT gcvUSER_SIGNAL_DESTROY gcvSURF_X32B32G32R32UI_2_G32R32UI gcvSURF_X8L8V8U8_1_A8R8G8B8 gcvSURF_A8B8G8R8UI gcoOS_FreeVideoMemory gcvFEATURE_SH_HALF_DEPENDENCY_FIX gcvSURF_X1B5G5R5 gcvFEATURE_RA_CG_FIX _gcoSURF gcFEATURE_BIT_NN_HW_LIMITATION_NATIVE_KER_1x2_2x1 _gcsHAL_IMPORT_VIDEO_MEMORY gcvFEATURE_EVIS_NO_FILTER gcvSURF_B10G11R11F_1_A8R8G8B8 gcvHAL_SET_POWER_MANAGEMENT_STATE powerManagement gcvSURF_X8R8 dynamicTailSize gcvFEATURE_KERNEL_VIP_SRAM_READ_BW_LIMITATION_FIX gcvFEATURE_32F_COLORMASK_FIX G2D_CACHE_FLUSH g2d_rotation mcClk gcvFEATURE_XY_OFFSET_LIMITATION_FIX gcv2D_TSC_2D_COMPRESSED gcvFEATURE_2D_VMSAA gcvSTATUS_LOCKED _gcsRECT gcvFEATURE_2D_MAJOR_SUPER_TILE gcvSTATUS_INVALID_ADDRESS gcvFEATURE_HALTI0 gcvFEATURE_HALTI1 gcvFEATURE_HALTI2 gcvFEATURE_HALTI3 gcvFEATURE_HALTI4 gcvFEATURE_HALTI5 gcvBLOCK_VG gcvFEATURE_MC_FCCACHE_BYTEMASK _gcsVG_RECT gcFEATURE_BIT_BURST_COLLECT_DUMMY_DATA_WASTE_CYCLES_FIX gcvSURF_VERTEX long double g2d_format gcvHAL_QUERY_RESET_TIME_STAMP gcvFEATURE_PROBE gcvHAL_PROFILE_REGISTERS_2D _gcsHAL_LOCK_VIDEO_MEMORY gcvPROGRAM_STAGE_VERTEX gcvFEATURE_HELPER_INVOCATION _gceHARDWARE_TYPE _gcsHAL_COMMIT clusterAvailMask gcvHAL_TIMESTAMP gcvSTATUS_OUT_OF_SAMPLER gcvFEATURE_2D_YUV420_OUTPUT_LINEAR _gcsHAL_EXPORT_VIDEO_MEMORY gcv900 gcv1000 gcvFEATURE_DEBUG_MODE clipping2D gcvHAL_COMMIT_DONE gcvSURF_A8_SBGR8 gcvFEATURE_D24S8_SAMPLE_STENCIL gcvSURF_RENDER_TARGET_LINEAR gcvSURF_R5G5B5X1 gcvSURF_A2B10G10R10UI gcvPROGRAM_STAGE_GRAPHICS_COUNT _gcsHAL_WRITE_REGISTER gcvSURF_NV61 gcvSTATUS_INVALID_REQUEST _gcsHAL_CREATE_NATIVE_FENCE gcvFEATURE_HW_TFB channelId gcvSTATUS_UNDECLARED_VARYING gcvFEATURE_TX_MULTISAMPLER_FC_FIX desc gcvFEATURE_2D_ROTATION_STALL_FIX gcvFEATURE_TP_REAL_INT16 gcvFEATURE_2D_MULTI_SOURCE_BLT_EX gcvFEATURE_SINGLE_PIPE_HALTI1 virtAddr _gcsHAL_SUBCOMMIT gcvFEATURE_TX_HOR_ALIGN_SEL dst_planes asynchroneous gcvFEATURE_NN_FAST_FIRST_PIXEL_POOLING gcvFEATURE_TEX_CACHE_FLUSH_FIX gcvFEATURE_END_EVENT gcvSTATUS_LOCATION_NOTCONSISTENT validProcessID gcvKERNEL_COMMAND gcvSURF_MASK gcvSTATUS_TRUE QueryChipOptions shBuf AllocateNonPagedMemory gcvSURF_ASTC6x6_SRGB gcvHAL_LOCK_VIDEO_MEMORY gcvSURF_X4B4G4R4 gcvFEATURE_COMMAND_PREFETCH g2d_clear_2d gcvFEATURE_DXT_TEXTURE_COMPRESSION gcvTILED_4X8 gcvFEATURE_MC_STENCIL_CTRL gcvSURF_A32B32G32R32UI_2_G32R32F fc_value extSRAMGPUVirtAddrs gcvFEATURE_TX_DECOMPRESSOR gcvFEATURE_2D_TILESTATUS_ROTATION gcvFEATURE_INTEGER32_FIX G2D_RGB565 WaitNativeFence exitIndex gcvFEATURE_PIPE_CL gcvSURF_A8R8G8B8 ocl_context G2D_XBGR8888 gcvSURF_A16R16G16B16 gcv8000 gcvSURF_R32F_1_A8R8G8B8 mirrorExt gcFEATURE_BIT_USE_SINGLE_PORT_VIPSRAM gcvFEATURE_EEZ gcvFEATURE_2D_V4COMPRESSION gcvFEATURE_BUG_FIXES2 gcvFEATURE_BUG_FIXES4 g2d_tiling gcvFEATURE_BUG_FIXES7 gcvFEATURE_BUG_FIXES8 gcv2D_STATE_XRGB_ENABLE gcvHAL_WRITE_DATA QueryVideoMemory gcvENGINE_GPU_ENGINE_COUNT gcoOS_CacheInvalidate G2D_ZERO gcvSURF_G32F gcvFEATURE_OCB_COUNTER gcvFEATURE_NN_FULLCACHE_KERNEL_INTERLEAVE_FIX gcvSURF_A12R12G12B12 gco2D_SetPixelMultiplyModeAdvanced gcvFEATURE_BUG_FIXED_IMPLICIT_PRIMITIVE_RESTART gcvFEATURE_SINGLE_BUFFER gcvINVALIDTILED gcvSTATUS_MEMORY_LOCKED gcvFEATURE_USC_GOS_ADDR_FIX coreId gcvSURF_B5G6R5 gcvHAL_SET_PROFILE_SETTING gcvFEATURE_2DPE20 chipFlags gcvFEATURE_FE_12bit_stride gcvFEATURE_SAMPLEPOS_SWIZZLE_FIX size_t gcvSURF_V16U16 frameInfo gcvKERNEL_VERTEX gcvFEATURE_PE_VMSAA_COVERAGE_CACHE_FIX gco2D_SetClipping gcvSURF_X32B32G32R32F_1_A8R8G8B8 gcvFEATURE_TP_ENGINE build gctFLOAT gcvFEATURE_NN_ENGINE _gcsHAL_QUERY_RESET_TIME_STAMP gcvSURF_G32R32F_1_A8R8G8B8 gcv2D_TSC_V4_COMPRESSED Logical gcvSURF_A32B32G32R32UI gcvSURF_TILE_STATUS_DIRTY gcvSURF_D32F gcvBLOCK_PIXEL gcvVG_BLEND_LIGHTEN __builtin_memcpy gcvFEATURE_NEW_STEERING_AND_ICACHE_FLUSH gcvSURF_ASTC8x5 gcvTILED gcoSURF_Destroy gcvFEATURE_DEC_COMPRESSION_TILE_NV12_10BIT gcvFEATURE_2D_TARGET_MAJOR_SUPER_TILE gcvSURF_A32R32G32B32_2_G32R32F gcvFEATURE_V2_MSAA_COHERENCY_FIX gcvFEATURE_LOADATTR_OOB_FIX gcvFEATURE_EVIS_ACCSQ_8OUTPUT layers gcvSTATUS_TOO_MANY_INPUT gcvFEATURE_ETC1_TEXTURE_COMPRESSION vidMem gcvFEATURE_ANDROID_ONLY gctUINT32_PTR gcvFEATURE_DITHER_AND_FILTER_PLUS_ALPHA_2D gcv2D_COLOR_MULTIPLY_DISABLE gcvSTATUS_TOO_MANY_ATTRIBUTES gcvSURF_ASTC10x5_SRGB gcvSRAM_EXT_COUNT _gco2D videoMode gcvSTATUS_CHIP_NOT_READY gcvSURF_ASTC12x12_SRGB gcvTILED_16X4 gcvSURF_B8G8R8_SNORM gcFEATURE_BIT_DEPTHWISE_16BIT_FORMAT gcFEATURE_BIT_V8_ACCUMLATION_READ_OUT_HAS_BUBBLES_PERF_FIX G2D_ONE gcvHAL_GET_GRAPHIC_BUFFER_FD gcvHAL_CONFIG_POWER_MANAGEMENT commandBuffer gcvFEATURE_TX_LOD_GUARDBAND gcvSTATUS_NAME_MISMATCH gcvFEATURE_TILEFILLER_32TILE_ALIGNED UserSignal gcvFEATURE_2D_A8_TARGET g2d_cache_op gcvFEATURE_YUV420_SCALER pool gcvSURF_R5G5B5A1UI gcvSURF_L8_RAW numConstants gcvFEATURE_2D_10BIT_OUTPUT_LINEAR stderr gcvHAL_WAIT_FENCE gcvBLOCK_TESSELLATOR2 gcvFEATURE_NN_INT16_ALU gcvSURF_B16G16R16UI _gcsHAL_FREE_NON_PAGED_MEMORY gcvSURF_G8R8I gcvFEATURE_NN_DEPTHWISE_SUPPORT g2d_surface_pair gcv2D_TSC_DISABLE G2D_BGRX5551 gcvSURF_D24S8 chipDate gcvFEATURE_DC gcvSURF_G8R8UI fc_enabled gcvSHBUF_MAP gcvSURF_A32B32G32R32I_1_A8R8G8B8 gcvVG_BLEND_DST_IN gcvSURF_SRGB8_PUNCHTHROUGH_ALPHA1_ETC2 DebugDump _gceFLATMAP_FLAG g2d_buf_context shared gcvSURF_X8G8R8UI gcvFEATURE_2D_CACHE_128B256BPERLINE gcvFEATURE_COMPRESSION available gcvSURF_DEPTH gcvSURF_X16B16G16R16 gco2D_SetFilterType gcvSURF_X16B16G16R16UI priority gcvVG_IMAGE_NORMAL gcvSURF_B10G11R11F gcvFEATURE_TP_FLOAT32_IO gcvFEATURE_SH_GM_ENDIAN gcvSURF_INDEX4 gcvMULTI_SUPERTILED gcvSURF_B5G5R5X1 useOpenCLBlit gcvFEATURE_EVIS_VX2 gcoVG_EnableDither gcvFEATURE_TX_LERP_PRECISION_FIX gcvFEATURE_BLT_YUV_OUTPUT gcvFEATURE_NN_ZDP3 dstRect gcvFEATURE_FULLCACHE_KERNELHEAD_FIX zones gcvSURF_ICACHE gcvSURF_A2L6 src_strides gcvFEATURE_WIDELINE_TRIANGLE_EMU gcvSURF_B32G32R32I gpuProfiler gcvFEATURE_SEPARATE_LS gcvFEATURE_EVIS_LERP_7OUTPUT _gcsHAL_CACHE gcvSURF_A16R16F gcvFEATURE_MEDIUM_PRECISION entryCount gcvSURF_A32B32G32R32F_4_A8R8G8B8 _gceCHIPPOWERSTATE _gcsHAL_GET_VIDEO_MEMORY_FD gcvFEATURE_IMGLD_WIDTH_LT16_FIX gcvSURF_L4 gcvFEATURE_2D_MULTI_SRC_BLT_TO_UNIFIED_DST_RECT gcvSTATUS_TOO_MANY_VARYINGS gcvSURF_L16_1_A4R4G4B4 gcvSURF_TXDESC gcvSURF_TILED smallBatch gcvSURF_A8B8G8R8I_1_A8R8G8B8 gco2D_SetROP callCommandSize gcvSURF_B4G4R4A4 g2d_multi_blit_2d gcvFEATURE_TP_SMALLBATCH_PHASE1 gcvSURF_A16B16G16R16_1_A8R8G8B8 gcvFEATURE_HZ gcvFEATURE_PA_FARZCLIPPING_FIX gcvFEATURE_TX_BORDER_CLAMP_FIX gcvFEATURE_2D_OPF_YUV_OUTPUT gcvSURF_D24X8 gcvSURF_A16B16G16R16 g2d_blit gcvSTATUS_NO_MORE_DATA gcvFEATURE_USC_BOTTLENECK_FIX gcvFEATURE_L2_CACHE_FOR_2D_420 flag gcvVG_BLEND_SRC_OVER gcvSURF_R5G6B5UI gcvFEATURE_MRT_FC_FIX gcvHAL_DEVICE_MUTEX gcvFEATURE_S8_MSAA_COMPRESSION gcvSURF_TFBHEADER gcvFEATURE_LS_SUPPORT_PER_COMP_DEPENDENCY buf_handle gcvFEATURE_FORMAT_YUV_I010 G2D_GLOBAL_ALPHA G2D_YUYV gcvSURF_NV12_10BIT gcvFEATURE_SH_ICACHE_ALLOC_COUNT_FIX G2D_HARDWARE_VG subRect isMutexLocked gcvSURF_POST_FLIP_X gcvSURF_POST_FLIP_Y g2dContext g2d_finish gcvFEATURE_TEXTURE_GATHER gpuCoreCount gcvFEATURE_2D_FC_SOURCE gpuIdle gcvFEATURE_TEXTURE_ARRAY gcvSURF_COLOR_LINEAR G2D_VYUY gcvSURF_G8R8UI_1_A4R4G4B4 gcvHAL_DETACH gcoOS_DestroySignal G2D_BLEND_DIM customerID gcvSTATUS_MISSING_OUTPUT_VERTEX_COUNT extSRAMIndex srcWidth gcvCOMPRESSION_OPTION_DEPTH gcvSURF_X16R16 extSRAMSizes gcoVG_Clear gcvFEATURE_2D_FILTERBLIT_FULLROTATION gcvSURF_X16R16F gcvSURF_X16R16I gcv4000 gcvHAL_DEC300_FLUSH_WAIT maxState _gce2D_GLOBAL_COLOR_MULTIPLY_MODE gcvSURF_X12R12G12B12 gcoOS_CacheFlush gcvSTATUS_NOT_FOUND gcvSURF_DXT1 gcvSURF_DXT2 gcvSURF_DXT3 gcvSURF_DXT4 gcvSURF_DXT5 userData nonPaged gcvKERNEL_TEXTURE gcvFEATURE_SPECIAL_MSAA_LOD gcvSTATUS_MEMORY_UNLOCKED gcvFEATURE_PE_DITHER_FIX2 _gcsHAL_CONFIG_POWER_MANAGEMENT gcv200 gctBOOL gcvSURF_A8B8G8R8 vFactor gcoSURF_SetOrientation _gcsFLAT_MAPPING_RANGE _gcsHAL_DETACH gcvSURF_G16R16_1_A8R8G8B8 gcvSURF_X16R16UI_1_A4R4G4B4 gcvSURF_B32F gcvFEATURE_8K_RT yuvMode gcvFEATURE_MAX_POINTSIZE_CLAMP _gcsHAL_SHBUF gcvSURF_TEXTURE_NO_VIDMEM gcvSURF_X24S8 gcvUSER_SIGNAL_MAP gcvHAL_QUERY_COMMAND_BUFFER dstGlobalAlphaMode gcvSURF_FENCE gcvFEATURE_IDLE_BEFORE_FLUSH_COMPLETE_FIX gcvFEATURE_TPC_COMPRESSION gcvSTATUS_TOO_COMPLEX gcoVG_EnableScissor gcvFEATURE_SH_ROBUSTNESS_FIX gcvFEATURE_TX_ASTC_MULTISLICE_FIX gcvFEATURE_MULTI_CLUSTER gcvSURF_R3G3B2_1_A8R8G8B8 gcvFEATURE_SH_GM_USC_UNALLOC _gceSRAM_INTERNAL gcvFEATURE_SWTILING_PHASE1 gcvFEATURE_SWTILING_PHASE2 gcvFEATURE_SWTILING_PHASE3 gcvSTATUS_INPUT_ARRAY_SIZE_MISMATCH gcvSTATUS_OUT_OF_RESOURCES gcvFEATURE_PIPE_VG gcvSURF_R16F gcvSTATUS_TIMEOUT gco2D_SetBitBlitMirror gcvFEATURE_NN_SLICE_PADDING_TO_64BYTE_ALIGN gcvSURF_INDEX1 gcvFEATURE_FC_FLUSH_STALL gcvSURF_INDEX8 gcv2D_STATE_ARRAY_DE_GAMMA _gce2D_TILE_STATUS_CONFIG gcvFEATURE_TX_BORDER_CLAMP internalPhysName gcvSURF_L32F_1_R32F gcvSURF_G32R32I_2_A8R8G8B8 processID gcvFEATURE_FE_COMPUREINDIRECT_SKIP_UNIFORM G2D_BGR888 gcvSURF_ASTC8x8_SRGB gcvSURF_A32R32F gcvLINEAR gcvSURF_PIXEL_ALPHA_INVERSED gcvBLOCK_COMMAND gcvHARDWARE_NUM_TYPES QueryPowerManagement command uscL1CacheRatio gcvCACHE_MEMORY_BARRIER gcvSURF_CMA_LIMIT gcvSURF_NUM_TYPES minValue gcvFEATURE_TEXTURE_ASTC_BASE_LOD_FIX /opt/samba/nxf39444/test/gpu-viv6/fsl_drv/g2d/source G2D_XRGB8888 gcvCHIP_FLAG_MSAA_COHERENCEY_ECO_FIX gcvSURF_R4G4B4A4 gcvFEATURE_ENDIAN_CONTROL gcvSURF_R3G3B2UI gcvSURF_X16B16G16R16I_2_A8R8G8B8 gcvSURF_YVYU gcvFEATURE_EVIS_NO_SELECTADD gcvFEATURE_LOGIC_OP gcvFEATURE_MULTI_CORE_BLOCK_SET_CONFIG buf_vaddr gcvFEATURE_BLT_8bit_256TILE_FC_FIX gcvBLOCK_VG2 gcvBLOCK_VG3 gcvFEATURE_64BPP_HW_CLEAR_SUPPORT gcvFEATURE_3D_TEXTURE gcvSURF_A4L4 gcvHAL_DUMP_GPU_STATE g2d_alloc GNU C17 10.3.0 -mfpu=neon -mfloat-abi=softfp -mthumb -mtune=cortex-a9 -mabi=aapcs-linux -mtls-dialect=gnu -march=armv7-a+simd -g -O2 -O2 -fstack-protector-strong -feliminate-unused-debug-types -fno-strict-aliasing -fPIC gcvTILED_8X8_XMAJOR gcvHAL_SIGNAL gcvFEATURE_TP_REORDER_FIX gcvFEATURE_2D_SUPER_TILE_V1 gcvFEATURE_2D_SUPER_TILE_V2 gcvFEATURE_2D_SUPER_TILE_V3 gcvHARDWARE_3D2D gcvFEATURE_NN_BF16_ALU gcvTILED_8X4 g2d_init_opencl gcvTILED_8X8 gcvFEATURE_SH_TEXLD_U_FIX gcvSURF_X16R16I_1_A4R4G4B4 gcvFEATURE_EVIS_NO_DP32 stateCommandSize gcvFEATURE_SUPPORT_GCREGTX gcvSTATUS_SHADER_VERSION_MISMATCH gcvFEATURE_TP_REORDER_LAYER_SUSPEND_FIX G2D_FLIP_V dstAlphaMode height gcvSTATUS_CS_NO_WORKGROUP_SIZE gcvFEATURE_DR_JD_DIFF_CONDITION_FOR_CACHELINE_MODE_PRE_FIX gcvSURF_BLEND_STRAIGHT fetchCommandSize gcvSURF_HIERARCHICAL_DEPTH G2D_YUV_BT_601 vg_surf gcvFEATURE_COUNT srcAlphaMode gcvSURF_E5B9G9R9 gcvSURF_X32R32F gcvFEATURE_KERNEL_PER_CORE_LESS_THAN_THIRD_COEF_BUFF_DEPTH_FIX gcvSURF_X32R32I gcvFEATURE_2D_NO_COLORBRUSH_INDEX8 gcFEATURE_BIT_INIMAGE_2DTILE_NOT_LESS_160PIXEL_FIX gcvFEATURE_ASYNC_FE_FENCE_FIX gcvFEATURE_IMG_ADDR_NOT_WRAP_IF_OVER_OCB_ADDR_FIX gcvFEATURE_TX_DESCRIPTOR gcv2D_STATE_PROFILE_ENABLE malloc G2D_FLIP_H BottomHalfUnlockVideoMemory gcFEATURE_BIT_NN_COMPRESSION_BYPASSS gco2D_SetGenericTarget gcvSURF_RGB8_ETC2 gcvSURF_B16G16R16UI_2_A8R8G8B8 uint64_t gcoHAL_Get2DEngine gcvFEATURE_FAST_MSAA _gcsCOMMAND_BUFFER_INFO gcvFEATURE_SH_CMPLX gcvFEATURE_TX_8bit_UVFrac gcvSURF_A2B10G10R10_1_A8R8G8B8 _gcsHAL_SIGNAL gcvSURF_R16 gcvSURF_X16G16R16 gco2D_FilterBlitEx2 G2D_I420 gcvSTATUS_CACHED gcvFEATURE_GEOMETRY_SHADER gcvFEATURE_TEX_CUBE_BORDER_LOD gcvFEATURE_SHADER_HAS_FLOOR gcvCORE_2D gcvSURF_270_DEGREE gcvVG_BLEND_DST_OVER gcvSURF_B5G6R5UI G2D_BGRX8888 G2D_ONE_MINUS_DST_ALPHA gcvSTATUS_SMALLER instructionCount gcvVG_IMAGE_STENCIL gcvFEATURE_TX_TILE_STATUS_MAPPING _gcsHAL_DEVICE_MUTEX ShBuf gcv2D_STATE_SUPER_TILE_VERSION srcAddress gcvHARDWARE_VG gcvVG_IMAGE_FILTER _gceSURF_GLOBAL_ALPHA_MODE gcvFEATURE_FE_START_VERTEX_SUPPORT gcvSURF_X8R8I_1_A4R4G4B4 commitStamp _gce2D_SUPER_TILE_VERSION gcoOS_CreateNativeFence G2D_YUV_BT_709FR gcvFEATURE_SH_SUPPORT_ALPHA_KILL dstWidth gcvSURF_A8B8G8R8_1_A8R8G8B8 gcoVG_EnableColorTransform gcvSURF_B8G8R8I blending gcvSURF_R32 gcvFEATURE_SH_CLOCK_GATE_FIX gcvSURF_A8L8_1_A8R8G8B8 gcvFEATURE_FULLLY_SUPPORT_INTEGER_BRANCH gcvSURF_A32B32G32R32F gcvFEATURE_TEX_ETC2 gcvSURF_A32B32G32R32I physName SetFscaleValue gcvFEATURE_ROBUSTNESS gcvFEATURE_MULTI_PIXELPIPES WrapUserMemory gcvSURF_ASTC8x5_SRGB G2D_DST_YUV gcvFEATURE_TEXTURE_ANISOTROPIC_FILTERING gcvFEATURE_FE_PATCHLIST_FETCH_FIX gcvSURF_A32B32G32R32F_1_A8R8G8B8 bufHandle gcv400 g2d_blit_vg engine2D gcFEATURE_BIT_TP_KERNEL_1BYTE_ALGIN gcvSURF_DEPTH_TS_DIRTY g2d_free gcvFEATURE_DRAW_INDIRECT gcvSTATUS_NOT_MULTI_PIPE_ALIGNED clipRect2D src_planes timeDelta gcoHAL_Destroy gcvSURF_X16B16G16R16UI_2_A8R8G8B8 gcv2100 gcvSURF_A16R16 gcvSURF_A16B16G16R16F_1_A8R8G8B8 clrWidth gcv410 vMirror gcvSURF_BLEND_ZERO gcvFEATURE_TP_COEF_COMPRESSION_ENHANCEMENT g2d_close_opencl gcvFEATURE_EVIS_NO_ABSDIFF _gceORIENTATION streamCount gcvFEATURE_TP_MAX_POOLING_STRIDE1 gcvFEATURE_VG20 gcvFEATURE_VG21 timeStamp _gceTEXTURE_SWIZZLE gcvFEATURE_SH_PSO_MSAA1x_FIX gcvFEATURE_2D_MIRROR_EXTENSION gcvSURF_A1B5G5R5UI gcvSHBUF_READ gcvSTATUS_TOO_MANY_OUTPUT gcvFEATURE_2D_PIXEL_ALIGNMENT _gceSURF_FORMAT gctUINT32 numStates gcvFEATURE_FE_DRAW_DIRECT gcv420 pixelPipes operation gcvHAL_UNLOCK_VIDEO_MEMORY gcv428 gcvFEATURE_PE_DEPTH_ONLY_OQFIX g2d_query_feature gcv2D_STATE_ARRAY_YUV_DST_TILE_STATUS_ADDR gco2D_SetSourceTileStatus gcvSURF_X32R32UI gcvSURF_A16B16G16R16I_1_G32R32F gcvSHBUF_DESTROY gcvFEATURE_RTT WriteData gcvSURF_CACHEABLE_BITMAP global_alpha gcvCACHE_FLUSH gcvFEATURE_MULTIGPU_SYNC_V2 gcvFEATURE_MULTIGPU_SYNC_V3 flatMappingRanges _gcsHAL_GET_FRAME_INFO tmpRect gcvSTATUS_GPU_NOT_RESPONDING gcvFEATURE_TX_DXT gcvSTATUS_NEED_CONVERSION gcvSURF_ASTC10x5 gcvSURF_ASTC10x6 gcvSURF_ASTC10x8 gcvFEATURE_SHADER_HAS_CEIL gcvFEATURE_2D_YUV_MODE bufctx gcvSURF_R11_EAC gcvSURF_Q8W8V8U8_1_A8R8G8B8 gcvSURF_X32B32G32R32UI_3_A8R8G8B8 gcvSURF_L16F G2D_PRE_MULTIPLIED_ALPHA gcvSUPERTILED_256B gcvSURF_G32R32 gcvSURF_A32L32F_1_G32R32F gcvSURF_IMAGE gcvFEATURE_DEC_COMPRESSION gcv2D_GLOBAL_COLOR_MULTIPLY_COLOR coreIndex gcvFEATURE_TX_SNORM_SUPPORT gcvSURF_R8I gcvSURF_ASTC12x10_SRGB gcoVG_EnableMask G2D_CACHE_INVALIDATE gcvFEATURE_SEPARATE_SRC_DST gctUINT64 gcvFEATURE_ZCOMPRESSION gcvSTATUS_INVALID_ARGUMENT G2D_YUV_BT_709 restartCommandSize gcv450 gcvFEATURE_LINE_DIAMOND_RULE_FIX gcvFEATURE_2D_POST_FLIP gcvSURF_A2R10G10B10 _gcsHAL_NAME_VIDEO_MEMORY gcvSURF_COLOR_UNKNOWN gcvSURF_I12 gcvFEATURE_2D_CC_NOAA_SOURCE gcvSURF_ASTC5x4 gcvSURF_ASTC5x5 gcvSTATUS_DEVICE gcvFEATURE_SHADER_HAS_ATOMIC DebugLevelZone gcvSURF_SBGR8 gcvFEATURE_VERTEX_INST_ID_AS_ATTRIBUTE gcvFEATURE_SH_SNAP2PAGE_MAXPAGES_FIX gcvSTATUS_SSBO_MISMATCH gcoHAL_SetHardwareType gcvSTATUS_INVALID_INDEX gcvFEATURE_422_TEXTURE_COMPRESSION _gcoOS gcvFEATURE_NN_SMALLBATCH gcv7000 gcvSTATUS_MIPMAP_TOO_LARGE dstRot gcvFEATURE_TX_FLUSH_L1CACHE tsEnabled gcvFEATURE_R8_UNORM G2D_RGBX8888 timeOut g2d_hardware_type gcvSURF_B10G10R10A2 gcvFEATURE_2D_BITBLIT_FULLROTATION ChipInfo gcvFEATURE_NO_USER_CSC gcvSURF_X8_SBGR8 gcvSURF_R16UI_1_A4R4G4B4 gcvFEATURE_COEF_DELTA_CORD_OVERFLOW_ZRL_8BIT_FIX extSRAMCPUPhysAddrs gcvENGINE_CPU gcvPOWER_OFF_BROADCAST _gceCHIP_FLAG subCommit gcvSURF_X16R16G16B16_2_A8R8G8B8 gcvFEATURE_CL_PS_WALKER gcvFEATURE_MULTI_SOURCE_BLT gcvFEATURE_AI_GPU gcvSURF_A2R2G2B2 gcvSURF_TILE_STATUS g2d_tile_status G2D_TILED_STATUS timer gcvHAL_GET_PROFILE_SETTING gcvFEATURE_PIPELINE_32_ATTRIBUTES gcvFEATURE_FAST_CLEAR_FLUSH gcvFEATURE_LOW_EFFICIENCY_OF_ID_WRITE_IMGBUF_FIX gcvFEATURE_SHADER_HAS_RTNE gcvSURF_G16R16UI_1_A8R8G8B8 gcvSRAM_INTERNAL1 gcvFEATURE_NN_NO_Z_LOCATION_OFFSET G2D_STATUS_OK _gcsHAL_GET_BASE_ADDRESS gcvFEATURE_NN_PER_CHANNEL_QUANT gcvFEATURE_COLOR_COMPRESSION _gcsHAL_VIDEO_MEMORY_METADATA gcvFEATURE_RECT_PRIMITIVE buf_paddr gcvSURF_YUV420_TILE_10_ST G2D_SRC_YUV auxSignal gcvFEATURE_BLT_ENGINE gcvSURF_X8B8G8R8I gcvPOWER_IDLE_BROADCAST gcoSURF_SetBuffer gcvFEATURE_IMAGE_NOT_PACKED_IN_SRAM_FIX _gcsHAL_SET_POWER_MANAGEMENT allocCount gcvFEATURE_TX_FILTER gcoHAL_GetHardwareType extSRAMCount sRAMBases gcvSURF_YUY2 DestroyMmu _gceCOMPRESSION_OPTION gcvSURF_BLEND_COLOR gcvSURF_BLEND_COLOR_NO_CROSS SetTimeOut G2D_ROTATION gcvFEATURE_SECURITY gcvSURF_X8R8G8B8 gcvSURF_ASTC12x10 eventCommandSize gcvSURF_ASTC12x12 gcvSURF_G32R32F_2_A8R8G8B8 gcvFEATURE_MRT_8BIT_DUAL_PIPE_FIX contextID gcoHAL_QueryChipIdentity ImportVideoMemory gcvPROGRAM_STAGE_TCS gcvSTATUS_TOO_MANY_SHADERS physicalAddress tsOverflowInt gcvSURF_COLOR_ALPHA_PRE gcvSURF_B32G32R32F gcvFEATURE_TP_SMALLBATCH gcvTEXTURE_SWIZZLE_0 gcvTEXTURE_SWIZZLE_1 chipMinorFeatures short unsigned int gcvTEXTURE_SWIZZLE_A gcvFEATURE_MSAA_TEXTURE gcv600 gcvSURF_X16B16G16R16F_2_A8R8G8B8 gcvTEXTURE_SWIZZLE_G g2d_surf gcvSURF_LINEAR gcvSURF_L32F _gcsHAL_QUERY_CHIP_IDENTITY gcvTEXTURE_SWIZZLE_R gcvSTATUS_MISSING_MAIN manualReset gcvTILING_Y_MAJOR OnError gcvSURF_180_DEGREE gcvPOWER_ON gcvHAL_RESET G2D_YV12 gcvFEATURE_TILE_FILLER gcvFEATURE_NN_SINGLEPORT_ACCUMBUFFER gcvCORE_3D3 gcvCORE_3D4 gcvCORE_3D5 gcvCORE_3D6 gcvCORE_3D7 gcvFEATURE_ZSCALE_FIX gcvFEATURE_COEF_COMPRESSION_ENHANCEMENT G2D_DST_ALPHA gcvFEATURE_WIDELINE_HELPER_FIX g2d_enable gcvFEATURE_YUV420_TILER gcv2D_GLOBAL_COLOR_MULTIPLY_ALPHA _gcoVG gcvPROGRAM_STAGE_TES gcvSTATUS_SKIP gcvVG_BLEND_FILTER level gcvSURF_A8_SRGB8 fc_value_upper gcvFEATURE_DUAL_RETURN_BUS gcvFEATURE_NO_FLUSH_USC_FIX entryPipe gcv620 gcvFEATURE_SUPPORT_MOVAI gcv2D_YUV_DST _gcuDATABASE_INFO gcvHAL_DATABASE _gceSURF_PIXEL_ALPHA_MODE G2D_AMPHION_TILED_10BIT gcvFEATURE_TX_SUPPORT_DEC _gcsHAL_EVENT_COMMIT gcvSURF_X8G8R8I gcvHAL_IMPORT_VIDEO_MEMORY gcvSURF_A32R32G32B32_4_A8R8G8B8 gcvSURF_R4G4B4A4UI G2D_BGRA8888 process gcvSURF_G8R8_1_X8R8G8B8 gcvSURF_LINEAR_NO_ALIGNMENT _gceSTATUS delta gcvFEATURE_SHADER_ENHANCEMENTS2 gcvFEATURE_SHADER_ENHANCEMENTS3 separated2D gcoVG_SetSolidPaint gcvSURF_X2R10G10B10 gcvHAL_DEC300_FLUSH address _gcsEXTERNAL_MEMORY_INFO gcvFEATURE_RSBLT_MSAA_DECOMPRESSION addressAlignment _gcsHAL_ALLOCATE_NON_PAGED_MEMORY gcvSURF_X32B32G32R32F gcvSURF_X32B32G32R32I wait QueryChipFrequency gcoHAL_IsFeatureAvailable gcvSURF_G32R32I_1_A8R8G8B8 gcvFEATURE_SPECIAL_ANTI_ALIASING gcvSURF_A16F gcvSTATUS_NON_INVOCATION_ID_AS_INDEX gcvSURF_R4G4B4X4 gcvFEATURE_TP_LRN gcvHAL_SET_IDLE gcvFEATURE_VARYING_PACKING_LIMITATION gcvSURF_S8D32F gcvFEATURE_PSIO_MSAA_CL_FIX gcvFEATURE_GENERIC_ATTRIB _gceHAL_COMMAND_CODES srcHeight signal gcvFEATURE_FAST_CLEAR gcvFEATURE_2D_FILTERBLIT_A8_ALPHA gcvHAL_EXPORT_VIDEO_MEMORY _gcsHAL_DEBUG_DUMP gcvSURF_X8B8G8R8_SNORM gcvSURF_CACHEABLE_BITMAP_NO_VIDMEM gcvSURF_Q16W16V16U16_1_A8R8G8B8 gcoOS_GetEnv gcvSURF_A16B16G16R16I_2_A8R8G8B8 float gcvSURF_B16G16R16I_2_A8R8G8B8 baseAddress vidMemPool gcvSURF_X8R8UI_1_A4R4G4B4 gcvSURF_A8L8 gcvSURF_RG11_EAC gcvFEATURE_MULTIDRAW_INDIRECT gcvHAL_CREATE_NATIVE_FENCE gcvFEATURE_MIXED_STREAMS unsigned char gcvFEATURE_COMPUTE_ONLY G2D_ROTATION_270 gcvVG_BLEND_SRC_IN gcvSURF_X8R8UI blit_size gcvFEATURE_UNIFIED_SAMPLERS gcvFEATURE_4BIT_INPUT gcvFEATURE_NEW_HZ vg_blit_filter _gcsHAL_COMMIT_DONE gcvFEATURE_BUG_FIXES10 gcvFEATURE_BUG_FIXES11 gcvFEATURE_BUG_FIXES12 gcvFEATURE_2D_TILING gcvFEATURE_BUG_FIXES18 gcvFEATURE_EVIS_NO_BITREPLACE gcv2D_YUV_601 gcv2D_TSC_ENABLE subd gcvHAL_READ_REGISTER gcvFEATURE_TX_INTEGER_COORDINATE gcvFEATURE_INTEGER_SIGNEXT_FIX gcvFEATURE_SCALER subs gctSTRING gcvFEATURE_IMAGE_LS_NO_FULLMASK_FIX gcvSURF_G32R32UI_1_G32R32F gcvSURF_A16B16G16R16_2_A8R8G8B8 G2D_AMPHION_TILED gcvHAL_DUMP_EVENT gcvFEATURE_VG_IMAGE_16K gcvFEATURE_IMG_INSTRUCTION g2d.c gcvPOWER_IDLE_TIMEOUT gcvFEATURE_V2_COMPRESSION_Z16_FIX gctSIZE_T gcvFEATURE_LOD_FIX_FOR_BASELEVEL gcvSURF_A32R32 gco2D_SetStretchFactors gcvTLS_KEY_OPENCL varyingsCount gcvFEATURE_PE_RGBA16I_FIX gcvSURF_G16R16 maxBytes blur gcvFEATURE_NN_FLOAT32_IO gcvVG_IMAGE_MULTIPLY gcvSURF_X16B16G16R16UI_1_G32R32F gcvHAL_RELEASE_VIDEO_MEMORY extSRAMGPUPhysNames gcvSTATUS_LARGER g2d_close gcvSURF_B16G16R16I_1_G32R32F gcvSURF_A2W10V10U10 gcvSURF_X16B16G16R16F_1_A8R8G8B8 gcvFEATURE_PE_DISABLE_COLOR_PIPE gcvSURF_R8I_1_A4R4G4B4 gcvFEATURE_ONE_PASS_2D_FILTER gcvFEATURE_DEC_COMPRESSION_TILE_NV12_8BIT gcvHAL_READ_ALL_PROFILE_REGISTERS_PART1 gcvHAL_READ_ALL_PROFILE_REGISTERS_PART2 gcvPOWER_OFF_TIMEOUT gcvCOMPRESSION_OPTION_DEFAULT pixBits ConfigPowerManagement gcv3000 gcvSURF_ASTC5x5_SRGB gcvSTATUS_NOT_SUPPORT_INTEGER gcvFEATURE_SHADER_HAS_SQRT gcvFEATURE_SH_SCATTER_GATHER LockVideoMemory dstGlobalAlpha g2d_create_fence_fd gcvCHIP_AXI_BUS128_BITS gcvFILTER_SYNC gcvSTATUS_LINK_INVALID_SHADERS UnmapMemory gcvTILING_X_MAJOR gcvSURF_SRGB8_ETC2 SetVidMemMetadata gcvFEATURE_MODULE_CG gcvFEATURE_NN_PER_CHANNEL_QUANT_ASYM _gceBLOCK gcvFLATMAP_SHIFT reservedHead G2D_DITHER gcoSURF_SetColorType gcvSRAM_INTER_COUNT gcvSURF_NO_TILE_STATUS VGCommit gcvTEXTURE_SWIZZLE_B gco2D_SetTargetGlobalColorAdvanced gcv2D_STATE_EN_GAMMA gcvSURF_A2B10G10R10UI_1_A8R8G8B8 gcvSRAM_INTERNAL0 gcvSURF_A32F gcvSURF_A8R8 gcvFEATURE_TESSELLATION gcvORIENTATION_TOP_BOTTOM gcv800 gctSIGNAL gcvSURF_D24S8_1_A8R8G8B8 fprintf gcvFEATURE_VIP_DEC400 clrcolor gcvSURF_G8R8_SNORM gcvSURF_X16R16UI G2D_HARDWARE_2D gcvPOWER_SUSPEND_BROADCAST gcvFEATURE_INDEX_FETCH_FIX gcvTLS_KEY_OPENGL gcvFEATURE_FE_ALLOW_STALL_PREFETCH_ENG gcvFEATURE_NN_BRICK_MODE gcvTILING_SWAP G2D_NV12 G2D_NV16 hMirror gcvFEATURE_BUFFER_INTERLEAVING gcvSURF_SRGB8_ALPHA8_ETC2_EAC gcv2500 gcvFEATURE_NN_FP16_ALU feBufferInt gcvSURF_BLEND_SRC_ALPHA_SATURATED gcvFEATURE_SUPPORT_MSAA2X gcvSURF_TEXTURE_LINEAR gcv2D_TSC_TPC_COMPRESSED_V11 _gceSECURE_MODE gcvCOMPRESSION_OPTION_MSAA_COLOR gcvCORE_3D_MAX gcvFEATURE_FRUSTUM_CLIP_FIX taskTable G2D_AMPHION_INTERLACED gcvFEATURE_SH_MULTI_WG_PACK gcvFEATURE_EVIS gcvFEATURE_NN_ZDP6 G2D_NV21 srcGlobalAlphaMode gcvSURF_R8G8B8A8UI enableMMU gcvSTATUS_CONTEXT_LOSSED gcvFEATURE_OUTPUT_CONVERT_UINT8_INT8_TO_UINT16_INT16_FIX ReadRegisterData g2d_sync_opencl gcvSURF_R8G8B8 gcvFEATURE_SMALL_BATCH gcvCORE_3D1 gcvCORE_3D2 gcoSURF_SetVideoBuffer hardwareType gcvSURF_90_DEGREE gcvSURF_A16B16G16R16UI gcvSURF_3D gcvSURF_X32B32G32R32I_3_A8R8G8B8 gcvSURF_X8G8R8 gcvFEATURE_CORRECT_STENCIL types gcvHAL_QUERY_CHIP_FREQUENCY gcvSURF_X32B32G32R32I_2_G32R32I gcvSURF_A16B16G16R16F gcvSURF_X8G8R8UI_1_A4R4G4B4 gcvSURF_A16B16G16R16I returnCommandSize gcvFEATURE_RENDER_ARRAY gcvFEATURE_PA_VARYING_COMPONENT_TOGGLE_FIX gco2D_SetYUVColorMode gcoHAL_ExportVideoMemory gcvFEATURE_SHADER_HAS_INSTRUCTION_CACHE gcvCOMPRESSION_OPTION_NONE gcvFEATURE_2D_ALL_QUAD gcvFEATURE_PARTLY_SUPPORT_INTEGER_BRANCH gcvFEATURE_BYTE_WRITE_2D gcoOS_GetBaseAddress gcvFEATURE_TEXTURE_ASTC gcvFEATURE_ADVANCED_BLEND_MODE_PART0 _gce2D_YUV_COLOR_MODE _gcsHAL_DESTROY_MMU yuv_mode logicals gcvFEATURE_TEXTURE_GATHER_OFFSETS gcvFEATURE_VG_FILTER gcvSURF_X8B8G8R8 gcoOS_GetCurrentProcessID contextSwitched gcvSURF_G32R32I_1_G32R32F gcvFEATURE_MMU G2D_SUPERTILED gcvHAL_SHBUF gcvFEATURE_NEW_RA gcvFEATURE_ADVANCED_BLEND_OPT gcvHAL_GET_FSCALE_VALUE gcvFEATURE_2D_COLOR_SPACE_CONVERSION count gcvSTATUS_VARYING_TYPE_MISMATCH gcvHAL_WRITE_REGISTER G2D_RGBX5551 gcvFEATURE_NEGATIVE_POST_SHIFT_FIX gcvSURF_B4G4R4X4 gcvFEATURE_CORRECT_AUTO_DISABLE_COUNT G2D_BLEND gcvFEATURE_CHIPENABLE_LINK shClk gcvFEATURE_TX_DESC_CACHE_CLOCKGATE_FIX _gcsHAL_CHIP_INFO gceENGINE contiguousPhysName gcvSURF_G32R32UI_1_A8R8G8B8 gcvFEATURE_TEXTURE_TILE_STATUS_READ G2D_NV61 gcvFEATURE_PE_NO_ALPHA_TEST gcvFEATURE_NN_NONZERO_MIRROR_BORDER gcvHARDWARE_INVALID _gceCACHEOPERATION gcvFEATURE_SH_IMG_LDST_CLAMP gcv860 gcv2D_SUPER_TILE_VERSION_V1 gcv2D_SUPER_TILE_VERSION_V2 gcv2D_SUPER_TILE_VERSION_V3 gcvFEATURE_MSAA gcvFEATURE_2D_A8_NO_ALPHA gcvSURF_NV21_10BIT gcvSURF_A2R10G10B10_1_A8R8G8B8 gcv7400 gcv2D_STATE_ARRAY_CSC_RGB_TO_YUV gcvFEATURE_COMPRESSION_V1 gcvFEATURE_COMPRESSION_V2 gcvFEATURE_COMPRESSION_V3 gcvFEATURE_COMPRESSION_V4 gcvFEATURE_BUG_FIXES1 gcvHAL_VERSION gcoSURF_Unlock gcvFEATURE_VMSAA gcvHAL_READ_PROFILER_REGISTER_SETTING gcvSURF_A8B12G12R12_2_A8R8G8B8 gcFEATURE_BIT_TPLITE_BFLOAT16 gcvFEATURE_NN_CONVOUT_FIFO_DEPTH_FIX gcvFEATURE_BUG_FIXED_INDEXED_TRIANGLE_STRIP information gcvFEATURE_TEXTURE_BUFFER gcvSTATUS_INVALID_CONFIG gcvSURF_A32R32G32B32_1_A8R8G8B8 gcvFEATURE_RS_YUV_TARGET gcvFEATURE_ZERO_ATTRIB_SUPPORT gcvSURF_CONTIGUOUS gcoVG_SetBlendMode gcvFEATURE_NN_BORDER_MODE gcv880 _gcsHAL_GET_FSCALE_VALUE gcvHAL_GET_VIDEO_MEMORY_FD gcvFEATURE_HIGH_DYNAMIC_RANGE gcvSURF_A8R3G3B2 gcvFILTER_USER gcoHAL_IsFeatureAvailable1 gcvFEATURE_SECURITY_AHB _gceKERNEL_WHERE gcvFEATURE_RA_DEPTH_WRITE gcvFEATURE_NN_ZDP_INIMAGE_SIZE_FIX gcvSTATUS_LOCATION_OVERLAP gcvSURF_TEXTURE_3D srcStride currentType gco2D_CalcStretchFactor g2d_buf_export_fd gctUINT gcvHAL_ATTACH gcvSURF_B8G8R8I_1_A8R8G8B8 gco2D_Clear gco2D_SetStateU32 gcvFEATURE_NN_SMALLBATCH_PHASE1 g2d_feature clrColor gcvTILED_8X8_YMAJOR G2D_ONE_MINUS_SRC_ALPHA gcvFEATURE_TF_QUANTIZATION gcvFEATURE_MSAA_FRAGMENT_OPERATION pixFormat gcvFEATURE_TX_INTEGER_COORDINATE_V2 gcvSURF_A32R32G32B32 gcvHAL_BOTTOM_HALF_UNLOCK_VIDEO_MEMORY _gcsHAL_QUERY_COMMAND_BUFFER gco2D_SetTarget gcvSURF_RGB8_PUNCHTHROUGH_ALPHA1_ETC2 gcvFEATURE_TP_REORDER gcvSURF_X24S8_1_A8R8G8B8 gcvFEATURE_PSCS_THROTTLE gcvFEATURE_ADVANCED_SH_INST gcvFEATURE_SRGB_RT_SUPPORT gcvCORE_VG gcoHAL_Flush gcvFEATURE_SMALL_MSAA _gceUSER_SIGNAL_COMMAND_CODES gcvSTATUS_COMPILER_FE_PARSER_ERROR gcvSURF_CREATE_AS_TEXTURE gcvFEATURE_PSIO_DUAL16_32bpc_FIX gcvFEATURE_COMPUTE_INDIRECT gcvFEATURE_2D_MULTI_SOURCE_BLT_EX2 gcvFEATURE_PSIO_INTERLOCK gcvFEATURE_DRAW_ID sRAMIndex gcvFEATURE_HIGHP_VARYING_SHIFT gcvFEATURE_HALF_FLOAT_PIPE gcvFEATURE_USC_DEFER_FILL_FIX gcvFEATURE_IMG_POP_PIPELINE_PAUSE_FIX gcvFEATURE_CORRECT_TEXTURE_CONVERTER WaitFence gcvSURF_TILE_RLV_FENCE gcvFEATURE_MULTIVIEW_RENDER gcvFEATURE_TP_BFLOAT16 _G2D_VERSION sRAMSizes gcv2D_YUV_USER_DEFINED gcvFEATURE_2D_DITHER gcvFEATURE_2D_FILTERBLIT_PLUS_ALPHABLEND gcvMINORTILED gcvSURF_I010 gcoHAL_Commit gcvFEATURE_FE_BASEINSTANCE gco2D_SetSource clrRect gcvSURF_ETC1 readback gcvPROGRAM_STAGE_LAST gcvSURF_B16G16R16 addressMask _gcsDATABASE_COUNTERS G2D_BGRA5551 dmabuf QueryResetTimeStamp node gcvSURF_A2B10G10R10 gcvFEATURE_TX_MIPFILTER_NONE_FIX gcvHAL_QUERY_CHIP_IDENTITY coreIndexs gcvSURF_A16B16G16R16F_2_A8R8G8B8 gcvFEATURE_TEXTURE_10_10_10_2 engineVG gcvSTATUS_TOO_MANY_UNIFORMS gcvFEATURE_VERTEX_INST_ID_AS_INTEGER dstDemultDstAlpha gcvFEATURE_HWMANAGED_LS gcvFEATURE_2D_SUPER_TILE_VERSION gcvSURF_Q16W16V16U16 gcvFEATURE_DANGLING_VERTEX_FIX g2d_cache_mode gcvSURF_A4R4G4B4 _gcsHAL_SET_FSCALE_VALUE g2d_construct_vg_surface G2D_YUV_BT_601FR gcoVG_SetTarget shValue gcvSTATUS_RECOMPILER_CONVERT_UNIMPLEMENTED gcvSURF_D16 gcvSURF_AYUV externalSize gcFEATURE_BIT_TP_ACCESS_VIPSRAM_OT_IS_ONE_FIX gcv2D_GLOBAL_COLOR_MULTIPLY_DISABLE gcvFEATURE_CORRECT_AUTO_DISABLE_COUNT_WIDTH gcvHAL_ALLOCATE_LINEAR_VIDEO_MEMORY gcFEATURE_BIT_MAX_TILE_SIZE gcvSURF_BITMAP_NO_VIDMEM gcvFEATURE_DRAW_ELEMENTS_BASE_VERTEX G2D_STATUS_NOT_SUPPORTED gcvSURF_V8U8 g2d_clear short int gcvSRAM_EXTERNAL0 gcvSRAM_EXTERNAL1 gcvTILED_64X4 gcvFEATURE_FENCE gcv2D_STATE_DEC_TPC_NV12_10BIT gcvSURF_B16G16R16F gcvSURF_ASTC8x6_SRGB gcvSURF_B16G16R16I gcvFEATURE_FENCE_64BIT G2D_SCALING gcvHAL_EVENT_COMMIT gcvFEATURE_BIT_INIMG_NOT_64BYTE_ALIGN_CACHELINE_MODE_FIX resolvePipes gco2D_EnableAlphaBlendAdvanced gcvFEATURE_DEC400EX_COMPRESSION ecoID gcvSURF_P010 _gcsHAL_VGCOMMIT dstFormat gcvSURF_X32G32R32 gctINT32 gcvTLS_KEY_OPENVG engine g2d_clear_vg enableSwtilingPhase1 gcoHAL_Construct gcvSURF_RENDER_TARGET_NO_TILE_STATUS gcvFEATURE_TEXTURE_YUV_ASSEMBLER gcvTLS_KEY_OPENVX gcvSURF_D32 gcvSURF_L6V5U5 gcvFEATURE_NEED_FIX_FOR_CL_XE gctINT gcvFEATURE_SH_SUPPORT_V4 gcvSURF_GLOBAL_ALPHA_SCALE gcvPOWER_IDLE gcvSURF_X32B32G32R32F_2_G32R32F gcvHAL_CHIP_INFO gcvSURF_A1 width gcvSURF_A4 CommitDone gcvSURF_A8 GetVideoMemoryFd Cache srcPremultGlobalMode gcvHAL_DEC300_READ gcvPROGRAM_STAGE_COMPUTE fromWhere gcvSURF_BLEND_ONE cacheable gcvHARDWARE_VIP srcGlobalAlpha dstPremultDstAlpha gcvSURF_B8 gcvVG_BLEND_SCREEN _gceFEATURE gcvSURF_X8L8V8U8 gcvSTATUS_LINK_LIB_ERROR gcvFEATURE_SH_IO_CG_FIX gcvSURF_X16B16G16R16F gcvSURF_X16B16G16R16I gcv2D_TSC_V4_COMPRESSED_256B reserved gcvSURF_B32G32R32UI_3_A8R8G8B8 gcvSURF_A2W10V10U10_1_A8R8G8B8 gcvFEATURE_SUPER_TILED gcvSURF_NV61_10BIT gcoVG_SetColorTransform g2d_disable gcvFEATURE_TEXTURE_SWIZZLE gcvFEATURE_SNAPPAGE_CMD_FIX hasShader gcvFEATURE_VIP_V7 _gcsHAL_WRITE_REGISTER_EX g2d_status gcvSURF_X8B8G8R8UI gcvSURF_X32R32 _gcsHAL_WRAP_USER_MEMORY dst_surface gcvSURF_B8G8R8 gcvSURF_RENDER_TARGET gcvSURF_R16I gcoOS_CreateSignal gcvFILTER_BLUR G2D_CACHE_CLEAN gcvFEATURE_SH_NO_ONECONST_LIMIT vg_blend_mode gcvFEATURE_SH_IDIV0_SWZL_EHS gcvSURF_G16R16F gcvSUPERTILED gcvSURF_G16R16I gcvFEATURE_PE_TILE_CACHE_FLUSH_FIX gcvFEATURE_MC20 counters oldValue src_surface start gcvFEATURE_YUY2_AVERAGING gcvSTATUS_NOT_ALIGNED gcvSURF_A32B32G32R32UI_1_A8R8G8B8 gcvPOWER_SUSPEND g2d_query_cap gcvSURF_G32R32UI gcv2D_COLOR_MULTIPLY_ENABLE logical gcvFEATURE_2D_COMPRESSION gcvSURF_B32G32R32 gcvHAL_DUMP_GPU_PROFILE g2d_surfaceEx _gcsHAL_QUERY_CHIP_OPTIONS gcvSURF_RG16 gcvSURF_W11V11U10 SourceMask gcvVG_BLEND_SRC gcvFEATURE_BLIT_COMPRESS_DEST srcRot g2d_copy srcG2dTiling gcoSURF_Lock _gcsHAL_USER_SIGNAL gcvFEATURE_FE_ROBUST_FIX state gcvSTATUS_TERMINATE gcvSURF_A16B16G16R16UI_1_G32R32F srcTile gcvFEATURE_SH_MULTI_WG_PACK_FIX gcvSURF_FLIP_X gcvSURF_FLIP_Y endCommandSize GetFscaleValue gcv2D_TSC_DEC_COMPRESSED gcvHAL_WRITE_REGISTER_EX compress_format gcvFEATURE_SHADER_HAS_TRIG gcvSURF_X2B10G10R10 gcvSURF_G8 gcvSURF_X32G32R32UI freeCount _gcsHAL_QUERY_VIDEO_MEMORY dstEx gcvSURF_G16R16F_1_A8R8G8B8 gcvSTATUS_NOT_SUPPORTED g2d_open gcvSURF_ASTC10x10_SRGB gcvFEATURE_DEC400_COMPRESSION gcvSURF_B32G32R32I_3_A8R8G8B8 gco2D_SetGenericSource gcvFEATURE_128BTILE gcvFEATURE_PE_A8B8G8R8 gcvSURF_R16UI gcvSURF_CXV8U8 gcvFEATURE_SH_END_OF_BB gcvSURF_INDEX time gcvSURF_SIGNED_R11_EAC gcvFEATUER_IMAGE_PARTIAL_CACHE _gcsHAL_ATTACH allowCompression alignment fenceFD gcvSURF_I4 gcvUSER_SIGNAL_UNMAP gcvSURF_I8 gcvFEATURE_USC_STAY_LRU gcvUSER_SIGNAL_WAIT gcvSURF_P010_LSB gcvSURF_A8L8_RAW G2D_SRC_ALPHA _gceCORE totalBytes gcvPOWER_ON_AUTO gcvFEATURE_RS_DS_DOWNSAMPLE_NATIVE_SUPPORT isOCLEnabled gcvSURF_A16R16G16B16_2_A8R8G8B8 g2d_query_hardware gcvSURF_A1B5G5R5 _gceSRAM_EXTERNAL staticTailSize left gcvSTATUS_NOT_SUPPORT_DITHER gcvFEATURE_NN_XYDP0 gcvSURF_R32UI_1_A8R8G8B8 gcvSECURE_NONE gcvFEATURE_NN_XYDP6 gcvFEATURE_NN_XYDP9 gcFEATURE_BIT_FAST_DP3_PREPROCESSOR gcvSURF_VYUY physical gcvFEATURE_PRIMITIVE_RESTART gco2D_StretchBlit gcvSURF_R8G8B8A8 gcvSHBUF_WRITE gcvSTATUS_INTERRUPTED gcvCOMPRESSION_OPTION_MSAA_DEPTH Version gcvFEATURE_SUPPORT_INTEGER gcvKERNEL_BLT blendfunc srcStrideNum Attach gcvFEATURE_TEXTURE_ASTC_DECODE_FIX gcvSTATUS_MISMATCH gcvFEATURE_BLOCK_SIZE_16x16 gcvSURF_TEXTURE physAddr gcvHAL_ALLOCATE_NON_PAGED_MEMORY gcvSURF_R32F gcvSTATUS_EXECUTED gcvSURF_R32I g2d_cap_mode gcvFEATURE_NEED_FIX_FOR_CL_X _gceCHIPMODEL gcvFEATURE_PSIO_SAMPLEMASK_IN_R0ZW_FIX baseAddress2D gcvSURF_BLEND_COLOR_INVERSED gcvSTATUS_TIMER_OVERFLOW gcvFEATURE_FENCE_32BIT gcvFEATURE_SUPPORT_INTEGER_ATTRIBUTE gcvSURF_L1 gcFEATURE_TP_REORDER_INTILE_X_SIZE_512_FIX hasVGPipe gcvSURF_L8 gcvFEATURE_NN_POWER_ISOLATION gcvSURF_G8R8G8B8 clrStride _gceTLS_KEY filterblit gcFEATURE_BIT_V8_SINGLE_PORT_ACCUMULATION_BUFFER_RW_CONFICT_ZERO_SKIP_PERF_FIX gcvFEATURE_TPCV11_COMPRESSION gcvSURF_G32R32F gcvSURF_G32R32I gcvBLOCK_TESSELLATOR3 gcvFEATURE_VERTEX_10_10_10_2 gcvSURF_DEPTH_NO_TILE_STATUS gcvSURF_A32B32G32R32UI_2_G32R32UI gcvSURF_ASTC4x4 startOffset gcvFEATURE_LINEAR_RENDER_TARGET gco2D_SetSourceGlobalColorAdvanced gcvSURF_G8R8I_1_A4R4G4B4 gcvSURF_YUV420_10_ST gcvFEATURE_INDEX_CONST_ON_B0 gcvSURF_R8_SNORM gcvPOWER_FLAG_TIMEOUT gcvSURF_A16L16 gcvFEATURE_BLT_64bpp_MASKED_CLEAR_FIX gcvFEATURE_NN_NATIVE_STRIDE_TWO gcvSURF_Q16W16V16U16_2_A8R8G8B8 gcvSURF_A16B16G16R16F_2_G16R16F gcvSURF_X8_SRGB8 gcvSURF_SCISSOR gcvFEATURE_USE_GL_Z gcvFEATURE_ASYNC_BLIT gcvHAL_DESTROY_MMU videoMemNode gcvSURF_I16 gcFEATURE_BIT_IMGLD_COMP_COUNT_FIX gcv2D_STATE_ARRAY_EN_GAMMA gcvUSER_SIGNAL_CREATE gcvHAL_UPDATE_DEBUG_CALLBACK gcvFEATURE_TS_FC_VULKAN_SUPPORT gcvSURF_BLEND_SRC_ALPHA_SATURATED_CROSS gcvSURF_X32G32R32F gcvSURF_X32G32R32I gcvFEATURE_VG_RESOLUTION_8K G2D_YVYU gcvMULTI_TILED gcvSURF_X32B32G32R32UI _gcsHAL_MAP_MEMORY gcvSURF_R8UI contiguousSize gcvFEATURE_DEPTH_MATH_FIX gcvSURF_A4B4G4R4 gcvFEATURE_SMALL_BATCH_FLOPS_RESET_FIX NameVideoMemory gcvFEATURE_NN_INTERLEAVE8 WriteRegisterData gcvFEATURE_CUBEMAP_ARRAY gcvTILED_32X4 bottom _HasAlpha gcvSURF_G16R16I_1_A8R8G8B8 g2d_blit_2d gcvFEATURE_PE_DITHER_COLORMASK_FIX _gcsHAL_READ_REGISTER_EX gcvSURF_X8R8I gco2D_DisableAlphaBlend g2d_blend_func _gcsHAL_INTERFACE gcvSURF_UNKNOWN gcvUSER_SIGNAL_SIGNAL QueryCommandBuffer gcuVIDMEM_NODE_PTR gcvFEATURE_STENCIL_TEXTURE gcvSURF_R8G8B8G8 chipRevision _gcsHAL_VERSION gcv300 dst_strides G2D_ABGR8888 gcvPROGRAM_STAGE_FRAGMENT gcvFEATURE_NN_LEAKY_RELU gcvSURF_ASTC6x5_SRGB gcvFEATURE_GS_SUPPORT_EMIT gcvFEATURE_2D_YUV_SEPARATE_STRIDE _gcsHAL_WAIT_NATIVE_FENCE gcoHAL_ScheduleEvent gcvFEATURE_USC_INVALIDATE_CACHE_LINE_FIX gcvFEATURE_VIP_SCALER gcvFEATURE_NN_ASYMMETRIC_INT8 gcvFEATURE_RA_DEPTH_WRITE_MSAA1X_FIX _gcsHAL_ALLOCATE_LINEAR_VIDEO_MEMORY gcvFEATURE_2D_MULTI_SRC_BLT_BILINEAR_FILTER gcvSURF_A1R5G5B5 gcv2000 gcvFEATURE_USC_ATOMIC_FIX2 gcvSURF_CACHEABLE _gceSURF_BLEND_FACTOR_MODE gcvSURF_R16I_1_A4R4G4B4 gcvSURF_BLEND_COLOR_INVERSED_NO_CROSS gcvHAL_SET_TIMEOUT gcvSURF_R8 _gceVG_IMAGE gco2D_SetCurrentSourceIndex sRAMCount gcvSTATUS_OUT_OF_MEMORY calloc gcvFILTER_LINEAR gcvFEATURE_MSAA_SHADING gcv320 gcvSURF_W11V11U10_1_A8R8G8B8 gcvSURF_ASTC10x8_SRGB gcv328 gcvSURF_DEC gcvFEATURE_PE_ENHANCEMENTS2 gcvFEATURE_SMALL_BATCH_DISBLE_FIX gcvHAL_USER_SIGNAL gcvFEATURE_EVIS_NO_IADD gcvSURF_S8 gcvHAL_QUERY_VIDEO_MEMORY commandAlignment gcvHAL_CACHE gcvFEATURE_TEX_SEAMLESS_CUBE dstFactorMode sync_cl gcvFEATURE_COMPRESSION_DEC400 gcvSURF_YUV420_TILE_ST gcvFEATURE_TX_UNNORMALIZED_COORD area gcvFEATURE_ENDIANNESS_CONFIG gcvFEATURE_NN_STRIDE_SUPPORT gcvSTATUS_HEAP_CORRUPTED gcvFEATURE_OUTIMAGE_X_BITWIDTH_LIMIT_FOR_NN_TRANSPOSE_FIX gcv1500 gcvSTATUS_MIPMAP_TOO_SMALL sRAMGPUVirtAddrs gcvSTATUS_CHANGED GetGraphicBufferFd gcvFEATURE_SAMPLER_BASE_OFFSET G2D_ROTATION_0 long long unsigned int gcvFEATURE_TX_8bit_UVFrac_ROUNDING_FIX gcvHAL_WAIT_NATIVE_FENCE gcvENGINE_BLT gcvFEATURE_NN_ZDP3_NO_COMPRESS_FIX gcvFEATURE_MULTI_CORE_BLOCK_SET_CONFIG2 gcvFEATURE_2D_FAST_CLEAR gcvHAL_GET_BASE_ADDRESS gcvSURF_R8UI_1_A4R4G4B4 gcvFEATURE_V1_COMPRESSION_Z16_DECOMPRESS_FIX gcv2D_TSC_DOWN_SAMPLER gcvSURF_I420 g2d_phys_addr_t gcvSURF_A32F_1_R32F flatMappingRangeCount gco2D_SetKernelSize gcvFEATURE_TILE_STATUS_2BITS gcvFEATURE_TEX_BASELOD gcvSTATUS_GENERIC_IO vKernel gcFEATURE_VALUE_DDR_KERNEL_BURST_SIZE dither gcvSTATUS_OK gcvFEATURE_NN_TRANSPOSE gcvFEATURE_EARLY_Z gcv350 gcv355 gcvFEATURE_DEPTH_BIAS_FIX contiguous gcvFEATURE_EXTRA_SHADER_INSTRUCTIONS0 gcvFEATURE_EXTRA_SHADER_INSTRUCTIONS1 gcvFEATURE_EXTRA_SHADER_INSTRUCTIONS2 gcvFEATURE_MULTICORE_CONFIG right buf_size _gceIMAGE_FILTER gco2D_Blit productID AllocateLinearVideoMemory gcvVG_BLEND_SUBTRACT gcvPOWER_INVALID gcvSURF_TYPE_UNKNOWN gcvSURF_BLEND_STRAIGHT_NO_CROSS gcvSURF_A8B8G8R8_SNORM _gcsHAL_READ_REGISTER gcvFEATURE_FE20_BIT_INDEX gcvFEATURE_64K_L2_CACHE gcvSURF_G8R8 gcvFEATURE_TEXTURE_8K gcvFLATMAP_DIRECT gcv2D_STATE_ARRAY_CSC_YUV_TO_RGB gcvSURF_B8G8R8A8 gcvFEATURE_USC_EVICT_CTRL_FIFO_FLOP_RESET_FIX gcvSURF_NO_VIDMEM gcvFEATURE_NN_CACHELINE_MODE_PERF_FIX allocatorName gcvFEATURE_USC_ASYNC_CP_RTN_FLOP_RESET_FIX G2D_MULTI_SOURCE_BLT perpixelAlpha chipMinorFeatures1 gcvVG_IMAGE_NONE chipMinorFeatures3 _gce2D_STATE chipMinorFeatures5 chipMinorFeatures6 gcvFEATURE_SH_FLAT_INTERPOLATION_DUAL16_FIX gcvFEATURE_TEXTURE_BIAS_LOD_FIX gcvSTATUS_MISSING_PRIMITIVE_TYPE gcvFEATURE_NN_ASYNC_COPY_PERF_FIX gcv2D_TSC_DEC_TPC_COMPRESSED gcv2D_TSC_COMPRESSED physAddress gcvFEATURE_ROBUST_ATOMIC DeviceMutex gcvFEATURE_DUAL_16 gcvFEATURE_MCFE gcvFEATURE_TX_YUV_ASSEMBLER_10BIT ReadRegisterDataEx srcBits gcvSURF_R10G10B10A2 gcvFEATURE_USC_ATOMIC_FIX WriteRegisterDataEx maxValue gcoOS_Destroy gcvSURF_A16B16G16R16UI_2_A8R8G8B8 ts_addr extSRAMGPUPhysAddrs gcvTLS_KEY_COUNT gcvFEATURE_2D_YUV_BLIT gcoOS_CacheClean gcvFEATURE_DYNAMIC_FREQUENCY_SCALING gcvFEATURE_NN_KERNEL_SIZE_WASTE_IN_PARTIAL_MODE_FIX gcvSURF_YV12 gcvENGINE_RENDER gcvSURF_G16R16UI gcvSHBUF_CREATE _gceFILTER_TYPE _gcsHAL_QUERY_POWER_MANAGEMENT gcvFEATURE_NN_REQ_SLOWARBITRATION_FIX gcvSTATUS_INVALID_OBJECT gcvSURF_G32R32UI_2_A8R8G8B8 gcoSURF_SetWindow _gcsHAL_RELEASE_VIDEO_MEMORY srcPremultSrcAlpha gcvSTATUS_DATA_TOO_LARGE gcv6400 gcvSURF_R8_1_X8R8G8B8 gcvPROGRAM_STAGE_GEOMETRY gctPOINTER _gceSHBUF_COMMAND_CODES gcvFEATURE_NEW_GPIPE supportedCL patch gcvFEATURE_BIT_NN_TP_INSTR_COMPLETE_IN_SAME_CYCLE_WITH_WAIT_EVENT_FIX gcvBLOCK_RASTER gcvTLS_KEY_OPENGL_ES gcvFEATURE_YUY2_RENDER_TARGET gcvSURF_B32G32R32F_3_A8R8G8B8 gcvYMAJOR_SUPERTILED chipMinorFeatures2 gcvSTATUS_INTERFACE_ERROR gcvKERNEL_TRIANGLE secureMode commitMutex gcvFEATURE_2D_MULTI_SRC_BLT_1_5_ENHANCEMENT clrHeight gcvFEATURE_NN_FLOAT_POST_MULT gcvHAL_UNMAP_MEMORY gcvSURF_NV16_10BIT gcvBLOCK_COUNT gcvSURF_CACHE_MODE_128 g2d_multi_blit isIdle gcvSURF_A16L16F __FUNCTION__ gcvVG_BLEND_MULTIPLY gcv500 gctUINTPTR_T gcvHAL_CONFIG_CTX_FRAMEWORK _gcsHAL_SET_DEBUG_LEVEL_ZONE gcvSURF_A12L12 G2D_TILED gcvENGINE_ALL_COUNT gcvFEATURE_SH_VX2_FLOATING_MAD_FIX gcvPOWER_SUSPEND_TIMEOUT gcvFEATURE_SNAPPAGE_CMD gcvSURF_DMABUF_EXPORTABLE G2D_DEMULTIPLY_OUT_ALPHA gcvSTATUS_LOCATION_ALIASED gcvFEATURE_PE_B2B_PIXEL_FIX gcvFEATURE_IMAGE_OUT_BOUNDARY_FIX gcv2200 gcv2D_TSC_DEC_TPC_TILED gcvSURF_A8B8G8R8UI_1_A8R8G8B8 gcvHAL_SET_FSCALE_VALUE gcvSURF_R5G5B5A1 gcvFEATURE_GPIPE_CLOCK_GATE_FIX gcvSURF_R10G10B10A2UI _gceTILING g2d_opencl_conversion externalPhysName gcvFEATURE_8K_RT_FIX gcvSURF_PIXEL_ALPHA_STRAIGHT vStride separatedVG SetPowerManagement gcvFEATURE_NN_FIRST_PIXEL_POOLING _gceSURF_ROTATION gcvFEATURE_ACE gcvSURF_NO_COMPRESSION blend_dim gcv520 gcoOS_DeviceControl gcvFEATURE_HAS_PRODUCTID gcvFEATURE_LINE_LOOP gcvFEATURE_2D_ONE_PASS_FILTER_TAP _gcsHAL_UNLOCK_VIDEO_MEMORY gcoVG_DrawImageFilter ReleaseVideoMemory gcvFEATURE_PSOUTPUT_MAPPING _gcsHAL_GET_GRAPHIC_BUFFER_FD gcv2D_STATE_MULTI_SRC_BLIT_BILINEAR_FILTER _gcsHAL_QUERY_CHIP_FREQUENCY _gceSURF_TYPE _gcsHAL_UNMAP_MEMORY gcvSTATUS_NAME_NOT_FOUND gcvSTATUS_INVALID_DATA gcv530 gcvSURF_B16G16R16F_2_A8R8G8B8 gcvSURF_A32B32G32R32I_2_G32R32F gcvSTATUS_NOT_OUR_INTERRUPT gcvSURF_A32B32G32R32I_2_G32R32I gcvFEATURE_SELECTMAP_SRC0_SWIZZLE_FIX gcvSTATUS_MORE_DATA gcvHAL_MAP_MEMORY gcvHAL_DEC300_WRITE gcvFEATURE_TEX_COMPRRESSION_SUPERTILED gcvSURF_SIGNED_RG11_EAC gcv2D_STATE_MULTI_SRC_BLIT_UNIFIED_DST_RECT gcvSURF_ASTC10x6_SRGB gcvFEATURE_FRAGMENT_PROCESSOR gcvFEATURE_MRT_TILE_STATUS_BUFFER dstTile chipFeatures gcFEATURE_BIT_TP_FC_FLOAT_LAST_PIXEL_NEGATIVE_0_FIX gcvSURF_X1R5G5B5 G2D_RGBA8888 gcFEATURE_BIT_BFP_COEF_AUTO_PAD_INCOMPLETE_ZERO_IN_KZ_PLANE gcvHAL_SET_VIDEO_MEMORY_METADATA gcv2D_YUV_USER_DEFINED_CLAMP gcvFEATURE_2D_SEPARATE_CACHE GetFrameInfo gcvFEATURE_32BPP_COMPONENT_TEXTURE_CHANNEL_SWIZZLE gcvSURF_ASTC4x4_SRGB chipMinorFeatures4 gcvSTATUS_UNIFORM_MISMATCH gcvSURF_S8D32F_1_G32R32F gcvFEATURE_DEC_TPC_COMPRESSION ts_fd gcvSURF_X32R32UI_1_A8R8G8B8 gcvSURF_X16R16G16B16 _gcsUSER_MEMORY_DESC gcvSTATUS_VERSION_MISMATCH gcvSURF_CREATE_AS_DISPLAYBUFFER gcvFEATURE_VG_DOUBLE_BUFFER gcvSURF_ASTC6x5 gcvSURF_ASTC6x6 gco2D_EnableDither Database gcvFEATURE_NN_CONV1x1_PERF_FIX memory gcvKERNEL_PIXEL timeout gcvSURF_X16G16R16UI gcvSURF_GLOBAL_ALPHA_OFF gcvFEATURE_TP_NN_PROBE gcvSURF_B32G32R32UI gcvCACHE_INVALIDATE gcvFEATURE_BIT_USC_INDIVIDUAL_PORT_WRT_EARLY_EVICT_DATA_CORRUPT_FIX gcvPROGRAM_STAGE_OPENCL gcvSURF_S8D32F_2_A8R8G8B8 G2D_STATUS_FAIL G2D_FAST_CLEAR _gce2D_PIXEL_COLOR_MULTIPLY_MODE gcvFEATURE_2D_MULTI_SOURCE_BLT gcvFEATURE_FULL_DIRECTFB gcvBLOCK_TESSELLATOR gcvCORE_COUNT coreSelect ignoreTLS gcvFEATURE_TEXTURE_FLOAT_HALF_FLOAT gcv2D_STATE_SPECIAL_FILTER_MIRROR_MODE srcFormat G2D_ROTATION_180 gcvFEATURE_SUPERTILED_TEXTURE g2d_make_current gcvFEATURE_NN_PER3DTILE_BUBBLE_FIX gcvFEATURE_WIDE_LINE gcvFEATURE_EVIS2_FLOP_RESET_FIX _IO_FILE __stack_chk_fail gctPHYS_ADDR_T gcvFEATURE_2D_ONE_PASS_FILTER exitPipe gcvSTATUS_UNIFORM_TYPE_MISMATCH gcvFEATURE_TP_23BITS_POST_MULTIPLIER gcvFEATURE_NN_TENSOR_ADD _gcoHAL gcvFEATURE_2D_GAMMA gcvFEATURE_FE_NEED_DUMMYDRAW gcvHAL_QUERY_POWER_MANAGEMENT_STATE gcoHAL_GetVGEngine gcvFEATURE_RS_NEW_BASEADDR gco2D_LoadSolidBrush gcv5000 gcvSURF_BLEND_INVERSED gcvSTATUS_NOT_SUPPORT_CL gcvSURF_R32I_1_A8R8G8B8 gcvSURF_X4R4G4B4 gcvSURF_A4B4G4R4UI gcvSURF_X32R32I_1_A8R8G8B8 g2d_surface _gcsHAL_SET_TIMEOUT gcvSTATUS_BUFFER_TOO_SMALL gcvFEATURE_TP_ROI_POOLING gcvCHIP_FLAG_GC2000_R2 G2D_ARGB8888 gcvSURF_A32L32F gcvFEATURE_PE_DITHER_FIX gcFEATURE_BIT_BFLOAT_COEF_COMPRESSION_ZERO_COEFBIT14_INVERSE Detach gcvSURF_R16F_1_A4R4G4B4 gcvFEATURE_USC_FULLCACHE_FIX global_alpha_enable srcPlanes gcvFEATURE_TP_SIMPLE_INT16 gcvFEATURE_HI_REORDER_FIX userClusterMask gcvFEATURE_PE_64bit_FENCE_FIX minor gcvSURF_R32UI gcvFEATURE_PIPE_2D gcvFEATURE_2D_MINOR_TILING gcvFEATURE_TX_LERP_LESS_BIT gcvHAL_FREE_NON_PAGED_MEMORY gcvSURF_A32B32G32R32UI_4_A8R8G8B8 gcv2D_TSC_DEC_TPC gcFEATURE_BIT_TILE_ACCESS_CAPABILITY iface gcvSURF_RGBA8_ETC2_EAC _gcsHAL_DATABASE MapMemory yuvBuffers gcvFILTER_BI_LINEAR gcvFEATURE_NN_COEF_DECOMPRESS_PERF2X gcvVG_BLEND_DARKEN gcvFEATURE_SH_IMG_LDST_ON_TEMP uStride current_type gcvFEATURE_FLIP_Y _gcePROGRAM_STAGE gcvFEATURE_TX_8BPP_TS_FIX platformFlagBits _gcsHAL_WRITE_DATA gcvHAL_SET_DEBUG_LEVEL_ZONE gcvFEATURE_PIPE_3D gco2D_MultiSourceBlit gcvFEATURE_HAS_OUTPUT_COUNT_FIX gcvFEATURE_VIP_SCALER_4K gcvHAL_DEC200_TEST gcvFEATURE_NN_SLOW_OUTPUT gcvHAL_WRAP_USER_MEMORY _gcuVIDMEM_NODE _gceVG_BLEND gcvFEATURE_SHADER_HAS_EXTRA_INSTRUCTIONS2 bytes srcEx G2D_ROTATION_90 gcoOS_AllocateVideoMemory gcvSURF_X8G8R8I_1_A4R4G4B4 gcvSURF_A8R3G3B2_1_A8R8G8B8 gcv700 gcvSURF_B16G16R16UI_1_G32R32F gcvFEATURE_EVIS_NO_BOXFILTER stretchblit gcvCACHE_CLEAN gcvSURF_X16G16R16F gcvSURF_X16G16R16I gcvFEATURE_TX_DEFAULT_VALUE_FIX gcvSURF_X32B32G32R32 strtol getSystemEnvInt getenv __errno_location prop os/linux/g2d_utils.c dma_buf_phys g2d_buf_from_virt_addr ion_fd query g2d_ion_phys_dma g2d_buf_from_fd dmafd ioctl os/linux/g2d_allocator.c __u64 strerror cl_ulong memDstU memDstV memDstY strlen clFlush clBuildProgram clCreateContext opencl_context _cl_device_id cl_mem_flags sizeSrcY kernel_string memSrcUV viv_phys_flags clEnqueueNDRangeKernel _cl_kernel clCreateBuffer memSrcY clFinish uint32_t cl_bitfield g_tile2linear_kernel kernel_10_to_8 clCreateKernel _cl_program kernel_read_row clReleaseProgram Init kernel_yuyv_to_nv12 _cl_platform_id global2d nPicHeight g2d_ocl.c kernel_yuyv_to_nv21 _cl_context exit cl_uint clCreateCommandQueue _cl_mem clReleaseMemObject devices clGetProgramBuildInfo cl_int g2d_opencl_kernel local2d platforms kernel_yuyv_to_yuv420 kernel_name clReleaseKernel clGetDeviceIDs cl_context_properties leftover clReleaseCommandQueue _cl_command_queue clReleaseContext clCreateProgramWithSource kernel_nv12_to_yuv420 clSetKernelArg sizeDstY clGetPlatformIDs offset2d dstStride
crti.o $a crtn.o crtstuff.c $d all_implied_fbits deregister_tm_clones __do_global_dtors_aux completed.1 __do_global_dtors_aux_fini_array_entry frame_dummy object.0 __frame_dummy_init_array_entry g2d.c g2d_construct_vg_surface $t g2d_copy.localalias __FUNCTION__.18 __FUNCTION__.23 __FUNCTION__.22 __FUNCTION__.21 __FUNCTION__.20 __FUNCTION__.19 __FUNCTION__.17 __FUNCTION__.16 __FUNCTION__.15 __FUNCTION__.14 __FUNCTION__.13 __FUNCTION__.12 __FUNCTION__.11 __FUNCTION__.10 __FUNCTION__.9 __FUNCTION__.8 __FUNCTION__.7 __FUNCTION__.6 __FUNCTION__.5 __FUNCTION__.4 __FUNCTION__.3 __FUNCTION__.2 __FUNCTION__.1 __FUNCTION__.0 g2d_utils.c g2d_allocator.c g2d_ocl.c __FRAME_END__ _DYNAMIC _GLOBAL_OFFSET_TABLE_ __dso_handle __TMC_END__ stderr ioctl gcoHAL_ScheduleEvent g_tile2linear_kernel gcoOS_CreateSignal gcoVG_SetColorTransform g2d_open gco2D_FilterBlitEx2 gcoHAL_Commit g2d_clear gcoOS_DestroySignal gco2D_SetYUVColorMode gcoOS_Construct _fini clReleaseCommandQueue@OPENCL_1.0 gco2D_SetROP clCreateCommandQueue@OPENCL_1.0 __deregister_frame_info clGetDeviceIDs@OPENCL_1.0 gcoHAL_Flush clBuildProgram@OPENCL_1.0 g2d_query_cap malloc g2d_opencl_conversion gcoSURF_Unlock gcoHAL_QueryChipIdentity gcoOS_StrCmp gcoSURF_SetOrientation gco2D_SetSource gcoSURF_SetColorType g2d_disable gco2D_Clear gcoOS_CreateNativeFence gco2D_EnableAlphaBlendAdvanced g2d_make_current gcoVG_SetBlendMode gco2D_SetGenericTarget gcoHAL_SetHardwareType gcoHAL_GetVGEngine g2d_close_opencl gcoOS_CacheFlush _ITM_deregisterTMCloneTable g2d_blitEx _init clEnqueueNDRangeKernel@OPENCL_1.0 gco2D_CalcStretchFactor g2d_init_opencl gcoHAL_ExportVideoMemory g2d_sync_opencl gcoVG_EnableColorTransform g2d_multi_blit gcoHAL_IsFeatureAvailable1 g2d_free g2d_alloc g2d_buf_from_virt_addr gcoSURF_Destroy gcoVG_Clear g2d_buf_export_fd isOCLEnabled g2d_create_fence_fd g2d_finish g2d_query_hardware gco2D_SetSourceTileStatus __stack_chk_guard gcoHAL_IsFeatureAvailable __cxa_finalize __register_frame_info clCreateContext@OPENCL_1.0 fprintf gco2D_SetPixelMultiplyModeAdvanced gcoOS_DeviceControl gcoOS_Destroy gco2D_LoadSolidBrush gco2D_SetKernelSize gcoOS_FreeVideoMemory gcoOS_CacheInvalidate gco2D_MultiSourceBlit clFlush@OPENCL_1.0 _ITM_registerTMCloneTable gcoVG_DrawImageFilter g2d_copy calloc clSetKernelArg@OPENCL_1.0 clReleaseContext@OPENCL_1.0 gco2D_DisableAlphaBlend g2d_enable gcoVG_EnableScissor clGetPlatformIDs@OPENCL_1.0 gco2D_SetTargetGlobalColorAdvanced gco2D_SetFilterType gco2D_SetCurrentSourceIndex gcoHAL_GetHardwareType gcoOS_CacheClean gco2D_Blit gco2D_StretchBlit g2d_flush __errno_location gcoOS_AllocateVideoMemory g2d_close gco2D_SetStretchFactors gcoSURF_Lock gco2D_SetGenericSource clGetProgramBuildInfo@OPENCL_1.0 gcoOS_GetCurrentProcessID clReleaseKernel@OPENCL_1.0 gcoVG_SetImageMode g2d_set_clipping clFinish@OPENCL_1.0 g2d_blit gcoOS_GetBaseAddress g2d_buf_from_fd gcoVG_SetSolidPaint _G2D_VERSION gcoSURF_ConstructWrapper gco2D_SetSourceGlobalColorAdvanced gco2D_EnableDither gcoVG_EnableDither gco2D_SetClipping clReleaseMemObject@OPENCL_1.0 clCreateProgramWithSource@OPENCL_1.0 strerror getSystemEnvInt gco2D_SetTarget gcoVG_SetTarget gcoHAL_Construct gcoHAL_Destroy getenv gcoSURF_SetBuffer gco2D_SetStateU32 clReleaseProgram@OPENCL_1.0 g2d_query_feature gcoVG_EnableMask gcoOS_GetEnv memcpy gcoSURF_SetVideoBuffer gcoHAL_Get2DEngine strlen strtol clCreateKernel@OPENCL_1.0 __stack_chk_fail g2d_cache_op clCreateBuffer@OPENCL_1.0 gcoSURF_SetWindow gco2D_SetBitBlitMirror
.symtab .strtab .shstrtab .gnu.hash .dynsym .dynstr .gnu.version .gnu.version_r .rel.dyn .rel.plt .init .text .fini .rodata .eh_frame .init_array .fini_array .dynamic .got .data .bss .comment .ARM.attributes .debug_aranges .debug_info .debug_abbrev .debug_line .debug_frame .debug_str .debug_loc .debug_ranges