Lines Matching defs:info
94 struct pipe_draw_info info;
429 (state->gs_output_lines == GS_OUTPUT_NONE && u_reduced_prim(state->info.mode) == PIPE_PRIM_LINES)))
570 state->dispatch_info.block[0] = pipeline->pipeline_nir[MESA_SHADER_COMPUTE]->info.workgroup_size[0];
571 state->dispatch_info.block[1] = pipeline->pipeline_nir[MESA_SHADER_COMPUTE]->info.workgroup_size[1];
572 state->dispatch_info.block[2] = pipeline->pipeline_nir[MESA_SHADER_COMPUTE]->info.workgroup_size[2];
925 state->info.mode = vk_conv_topology(ps->ia->primitive_topology);
929 state->info.primitive_restart = ps->ia->primitive_restart_enable;
1414 handle_descriptor(state, dyn_info, binding, stage, p_stage, i, descriptor->type, &descriptor->info);
1636 if (state->info.view_mask) {
1637 u_foreach_bit(i, state->info.view_mask)
1666 if (state->info.view_mask) {
1667 u_foreach_bit(i, state->info.view_mask)
1698 if (state->info.view_mask)
1790 struct pipe_blit_info info;
1791 memset(&info, 0, sizeof(info));
1793 info.src.resource = src_imgv->image->bo;
1794 info.dst.resource = dst_imgv->image->bo;
1795 info.src.format = src_imgv->pformat;
1796 info.dst.format = dst_imgv->pformat;
1797 info.filter = PIPE_TEX_FILTER_NEAREST;
1800 info.mask = PIPE_MASK_ZS;
1802 info.mask = PIPE_MASK_Z;
1804 info.mask = PIPE_MASK_S;
1807 info.sample0_only = true;
1809 info.sample0_only = true;
1811 info.src.box.x = state->render_area.offset.x;
1812 info.src.box.y = state->render_area.offset.y;
1813 info.src.box.width = state->render_area.extent.width;
1814 info.src.box.height = state->render_area.extent.height;
1815 info.src.box.depth = state->framebuffer.layers;
1817 info.dst.box = info.src.box;
1819 state->pctx->blit(state->pctx, &info);
1839 struct pipe_blit_info info;
1840 memset(&info, 0, sizeof(info));
1842 info.src.resource = src_imgv->image->bo;
1843 info.dst.resource = dst_imgv->image->bo;
1844 info.src.format = src_imgv->pformat;
1845 info.dst.format = dst_imgv->pformat;
1846 info.filter = PIPE_TEX_FILTER_NEAREST;
1847 info.mask = PIPE_MASK_RGBA;
1848 info.src.box.x = state->render_area.offset.x;
1849 info.src.box.y = state->render_area.offset.y;
1850 info.src.box.width = state->render_area.extent.width;
1851 info.src.box.height = state->render_area.extent.height;
1852 info.src.box.depth = state->framebuffer.layers;
1854 info.dst.box = info.src.box;
1856 info.src.level = src_imgv->vk.base_mip_level;
1857 info.dst.level = dst_imgv->vk.base_mip_level;
1859 state->pctx->blit(state->pctx, &info);
1956 const VkRenderingInfo *info = cmd->u.begin_rendering.rendering_info;
1957 bool resuming = (info->flags & VK_RENDERING_RESUMING_BIT) == VK_RENDERING_RESUMING_BIT;
1958 bool suspending = (info->flags & VK_RENDERING_SUSPENDING_BIT) == VK_RENDERING_SUSPENDING_BIT;
1961 vk_find_struct_const(info->pNext, MULTISAMPLED_RENDER_TO_SINGLE_SAMPLED_INFO_EXT);
1964 state->forced_depth_resolve_mode = info->pDepthAttachment ? info->pDepthAttachment->resolveMode : 0;
1965 state->forced_stencil_resolve_mode = info->pStencilAttachment ? info->pStencilAttachment->resolveMode : 0;
1972 state->info.view_mask = info->viewMask;
1973 state->render_area = info->renderArea;
1975 state->framebuffer.width = info->renderArea.offset.x +
1976 info->renderArea.extent.width;
1977 state->framebuffer.height = info->renderArea.offset.y +
1978 info->renderArea.extent.height;
1979 state->framebuffer.layers = info->viewMask ? util_last_bit(info->viewMask) : info->layerCount;
1980 state->framebuffer.nr_cbufs = info->colorAttachmentCount;
1982 state->color_att_count = info->colorAttachmentCount;
1984 for (unsigned i = 0; i < info->colorAttachmentCount; i++) {
1985 render_att_init(&state->color_att[i], &info->pColorAttachments[i]);
2000 render_att_init(&state->depth_att, info->pDepthAttachment);
2001 render_att_init(&state->stencil_att, info->pStencilAttachment);
2050 state->info.index_size = 0;
2051 state->info.index.resource = NULL;
2052 state->info.start_instance = cmd->u.draw.first_instance;
2053 state->info.instance_count = cmd->u.draw.instance_count;
2059 state->pctx->draw_vbo(state->pctx, &state->info, 0, NULL, &draw, 1);
2068 state->info.index_size = 0;
2069 state->info.index.resource = NULL;
2070 state->info.start_instance = cmd->u.draw_multi_ext.first_instance;
2071 state->info.instance_count = cmd->u.draw_multi_ext.instance_count;
2073 state->info.increment_draw_id = true;
2084 state->pctx->draw_vbo(state->pctx, &state->info, 0, NULL, draws, cmd->u.draw_multi_ext.draw_count);
2553 struct pipe_blit_info info;
2555 memset(&info, 0, sizeof(info));
2557 info.src.resource = src_image->bo;
2558 info.dst.resource = dst_image->bo;
2559 info.src.format = src_image->bo->format;
2560 info.dst.format = dst_image->bo->format;
2561 info.mask = util_format_is_depth_or_stencil(info.src.format) ? PIPE_MASK_ZS : PIPE_MASK_RGBA;
2562 info.filter = blitcmd->filter == VK_FILTER_NEAREST ? PIPE_TEX_FILTER_NEAREST : PIPE_TEX_FILTER_LINEAR;
2582 info.dst.box.x = dstX0;
2583 info.src.box.x = srcX0;
2584 info.dst.box.width = dstX1 - dstX0;
2585 info.src.box.width = srcX1 - srcX0;
2587 info.dst.box.x = dstX1;
2588 info.src.box.x = srcX1;
2589 info.dst.box.width = dstX0 - dstX1;
2590 info.src.box.width = srcX0 - srcX1;
2594 info.dst.box.y = dstY0;
2595 info.src.box.y = srcY0;
2596 info.dst.box.height = dstY1 - dstY0;
2597 info.src.box.height = srcY1 - srcY0;
2599 info.dst.box.y = dstY1;
2600 info.src.box.y = srcY1;
2601 info.dst.box.height = dstY0 - dstY1;
2602 info.src.box.height = srcY0 - srcY1;
2605 assert_subresource_layers(info.src.resource, &blitcmd->pRegions[i].srcSubresource, blitcmd->pRegions[i].srcOffsets);
2606 assert_subresource_layers(info.dst.resource, &blitcmd->pRegions[i].dstSubresource, blitcmd->pRegions[i].dstOffsets);
2609 info.dst.box.z = dstZ0;
2610 info.src.box.z = srcZ0;
2611 info.dst.box.depth = dstZ1 - dstZ0;
2612 info.src.box.depth = srcZ1 - srcZ0;
2614 info.dst.box.z = dstZ1;
2615 info.src.box.z = srcZ1;
2616 info.dst.box.depth = dstZ0 - dstZ1;
2617 info.src.box.depth = srcZ0 - srcZ1;
2620 info.src.box.z = blitcmd->pRegions[i].srcSubresource.baseArrayLayer;
2621 info.dst.box.z = blitcmd->pRegions[i].dstSubresource.baseArrayLayer;
2622 info.src.box.depth = blitcmd->pRegions[i].srcSubresource.layerCount;
2623 info.dst.box.depth = blitcmd->pRegions[i].dstSubresource.layerCount;
2626 info.src.level = blitcmd->pRegions[i].srcSubresource.mipLevel;
2627 info.dst.level = blitcmd->pRegions[i].dstSubresource.mipLevel;
2628 state->pctx->blit(state->pctx, &info);
2676 state->info.index_bounds_valid = false;
2677 state->info.min_index = 0;
2678 state->info.max_index = ~0;
2679 state->info.index_size = state->index_size;
2680 state->info.index.resource = state->index_buffer;
2681 state->info.start_instance = cmd->u.draw_indexed.first_instance;
2682 state->info.instance_count = cmd->u.draw_indexed.instance_count;
2684 if (state->info.primitive_restart)
2685 state->info.restart_index = util_prim_restart_index_from_size(state->info.index_size);
2692 state->info.index_bias_varies = !cmd->u.draw_indexed.vertex_offset;
2694 state->pctx->draw_vbo(state->pctx, &state->info, 0, NULL, &draw, 1);
2703 state->info.index_bounds_valid = false;
2704 state->info.min_index = 0;
2705 state->info.max_index = ~0;
2706 state->info.index_size = state->index_size;
2707 state->info.index.resource = state->index_buffer;
2708 state->info.start_instance = cmd->u.draw_multi_indexed_ext.first_instance;
2709 state->info.instance_count = cmd->u.draw_multi_indexed_ext.instance_count;
2711 state->info.increment_draw_id = true;
2713 if (state->info.primitive_restart)
2714 state->info.restart_index = util_prim_restart_index_from_size(state->info.index_size);
2728 state->info.index_bias_varies = !cmd->u.draw_multi_indexed_ext.vertex_offset;
2732 state->pctx->draw_vbo(state->pctx, &state->info, 0, NULL, draws, cmd->u.draw_multi_indexed_ext.draw_count);
2742 state->info.index_bounds_valid = false;
2743 state->info.index_size = state->index_size;
2744 state->info.index.resource = state->index_buffer;
2745 state->info.max_index = ~0;
2746 if (state->info.primitive_restart)
2747 state->info.restart_index = util_prim_restart_index_from_size(state->info.index_size);
2749 state->info.index_size = 0;
2756 state->pctx->draw_vbo(state->pctx, &state->info, 0, &state->indirect_info, &draw, 1);
3175 if (state->info.view_mask) {
3176 u_foreach_bit(i, state->info.view_mask)
3197 struct pipe_blit_info info;
3199 memset(&info, 0, sizeof(info));
3201 info.src.resource = src_image->bo;
3202 info.dst.resource = dst_image->bo;
3203 info.src.format = src_image->bo->format;
3204 info.dst.format = dst_image->bo->format;
3205 info.mask = util_format_is_depth_or_stencil(info.src.format) ? PIPE_MASK_ZS : PIPE_MASK_RGBA;
3206 info.filter = PIPE_TEX_FILTER_NEAREST;
3217 info.dst.box.x = dstX0;
3218 info.dst.box.y = dstY0;
3219 info.src.box.x = srcX0;
3220 info.src.box.y = srcY0;
3222 info.dst.box.width = resolvecmd->pRegions[i].extent.width;
3223 info.src.box.width = resolvecmd->pRegions[i].extent.width;
3224 info.dst.box.height = resolvecmd->pRegions[i].extent.height;
3225 info.src.box.height = resolvecmd->pRegions[i].extent.height;
3227 info.dst.box.depth = resolvecmd->pRegions[i].dstSubresource.layerCount;
3228 info.src.box.depth = resolvecmd->pRegions[i].srcSubresource.layerCount;
3230 info.src.level = resolvecmd->pRegions[i].srcSubresource.mipLevel;
3231 info.src.box.z = resolvecmd->pRegions[i].srcOffset.z + resolvecmd->pRegions[i].srcSubresource.baseArrayLayer;
3233 info.dst.level = resolvecmd->pRegions[i].dstSubresource.mipLevel;
3234 info.dst.box.z = resolvecmd->pRegions[i].dstOffset.z + resolvecmd->pRegions[i].dstSubresource.baseArrayLayer;
3236 state->pctx->blit(state->pctx, &info);
3245 state->info.index_bounds_valid = false;
3246 state->info.index_size = state->index_size;
3247 state->info.index.resource = state->index_buffer;
3248 state->info.max_index = ~0;
3250 state->info.index_size = 0;
3259 state->pctx->draw_vbo(state->pctx, &state->info, 0, &state->indirect_info, &draw, 1);
3284 union lvp_descriptor_info *info = &pds->infos[info_idx + j];
3289 info);
3335 union lvp_descriptor_info *info = &out_cmd->infos[descriptor_index + j];
3338 info->sampler = lvp_sampler_from_handle(in_cmd->descriptor_writes[i].pImageInfo[j].sampler);
3341 info->sampler = lvp_sampler_from_handle(in_cmd->descriptor_writes[i].pImageInfo[j].sampler);
3342 info->iview = lvp_image_view_from_handle(in_cmd->descriptor_writes[i].pImageInfo[j].imageView);
3343 info->image_layout = in_cmd->descriptor_writes[i].pImageInfo[j].imageLayout;
3348 info->iview = lvp_image_view_from_handle(in_cmd->descriptor_writes[i].pImageInfo[j].imageView);
3349 info->image_layout = in_cmd->descriptor_writes[i].pImageInfo[j].imageLayout;
3353 info->buffer_view = lvp_buffer_view_from_handle(in_cmd->descriptor_writes[i].pTexelBufferView[j]);
3360 info->buffer = lvp_buffer_from_handle(in_cmd->descriptor_writes[i].pBufferInfo[j].buffer);
3361 info->offset = in_cmd->descriptor_writes[i].pBufferInfo[j].offset;
3362 info->range = in_cmd->descriptor_writes[i].pBufferInfo[j].range;
3400 union lvp_descriptor_info *info = &pds->infos[info_idx + j];
3406 info);
3411 info);
3416 info);
3421 info);
3426 info);
3610 state->info.start_instance = cmd->u.draw_indirect_byte_count_ext.first_instance;
3611 state->info.instance_count = cmd->u.draw_indirect_byte_count_ext.instance_count;
3612 state->info.index_size = 0;
3616 state->pctx->draw_vbo(state->pctx, &state->info, 0, &state->indirect_info, &draw, 1);
3695 state->info.mode = vk_conv_topology(cmd->u.set_primitive_topology.primitive_topology);
3788 state->info.primitive_restart = cmd->u.set_primitive_restart_enable.primitive_restart_enable;