1/*
2 * Copyright © 2016 Red Hat.
3 * Copyright © 2016 Bas Nieuwenhuizen
4 *
5 * based in part on anv driver which is:
6 * Copyright © 2015 Intel Corporation
7 *
8 * Permission is hereby granted, free of charge, to any person obtaining a
9 * copy of this software and associated documentation files (the "Software"),
10 * to deal in the Software without restriction, including without limitation
11 * the rights to use, copy, modify, merge, publish, distribute, sublicense,
12 * and/or sell copies of the Software, and to permit persons to whom the
13 * Software is furnished to do so, subject to the following conditions:
14 *
15 * The above copyright notice and this permission notice (including the next
16 * paragraph) shall be included in all copies or substantial portions of the
17 * Software.
18 *
19 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
20 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
21 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL
22 * THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
23 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING
24 * FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS
25 * IN THE SOFTWARE.
26 */
27#ifndef RADV_ACO_SHADER_INFO_H
28#define RADV_ACO_SHADER_INFO_H
29
30/* this will convert from radv shader info to the ACO one. */
31
32#include "aco_shader_info.h"
33
34#define ASSIGN_FIELD(x) aco_info->x = radv->x
35#define ASSIGN_FIELD_CP(x) memcpy(&aco_info->x, &radv->x, sizeof(radv->x))
36
37static inline void
38radv_aco_convert_shader_so_info(struct aco_shader_info *aco_info,
39                       const struct radv_shader_info *radv)
40{
41   ASSIGN_FIELD(so.num_outputs);
42   ASSIGN_FIELD_CP(so.outputs);
43   ASSIGN_FIELD_CP(so.strides);
44   /* enabled_stream_buffers_mask unused */
45}
46
47static inline void
48radv_aco_convert_shader_vp_info(struct aco_vp_output_info *aco_info,
49				const struct radv_vs_output_info *radv)
50{
51   ASSIGN_FIELD_CP(vs_output_param_offset);
52   ASSIGN_FIELD(clip_dist_mask);
53   ASSIGN_FIELD(cull_dist_mask);
54   ASSIGN_FIELD(param_exports);
55   ASSIGN_FIELD(prim_param_exports);
56   ASSIGN_FIELD(writes_pointsize);
57   ASSIGN_FIELD(writes_layer);
58   ASSIGN_FIELD(writes_layer_per_primitive);
59   ASSIGN_FIELD(writes_viewport_index);
60   ASSIGN_FIELD(writes_viewport_index_per_primitive);
61   ASSIGN_FIELD(writes_primitive_shading_rate);
62   ASSIGN_FIELD(writes_primitive_shading_rate_per_primitive);
63   ASSIGN_FIELD(export_prim_id);
64   ASSIGN_FIELD(export_clip_dists);
65   /* don't use export params */
66}
67
68#define ASSIGN_OUTINFO(x) radv_aco_convert_shader_vp_info(&aco_info->x.outinfo, &radv->x.outinfo);
69static inline void
70radv_aco_convert_shader_info(struct aco_shader_info *aco_info,
71			     const struct radv_shader_info *radv)
72{
73   ASSIGN_FIELD(wave_size);
74   ASSIGN_FIELD(is_ngg);
75   ASSIGN_FIELD(has_ngg_culling);
76   ASSIGN_FIELD(has_ngg_early_prim_export);
77   ASSIGN_FIELD(num_tess_patches);
78   ASSIGN_FIELD(workgroup_size);
79   ASSIGN_OUTINFO(vs);
80   ASSIGN_FIELD(vs.as_es);
81   ASSIGN_FIELD(vs.as_ls);
82   ASSIGN_FIELD(vs.tcs_in_out_eq);
83   ASSIGN_FIELD(vs.tcs_temp_only_input_mask);
84   ASSIGN_FIELD(vs.use_per_attribute_vb_descs);
85   ASSIGN_FIELD(vs.vb_desc_usage_mask);
86   ASSIGN_FIELD(vs.has_prolog);
87   ASSIGN_FIELD(vs.dynamic_inputs);
88   ASSIGN_FIELD_CP(gs.output_usage_mask);
89   ASSIGN_FIELD_CP(gs.num_stream_output_components);
90   ASSIGN_FIELD_CP(gs.output_streams);
91   ASSIGN_FIELD(gs.vertices_out);
92   ASSIGN_FIELD(tcs.num_lds_blocks);
93   ASSIGN_OUTINFO(tes);
94   ASSIGN_FIELD(tes.as_es);
95   ASSIGN_FIELD(ps.writes_z);
96   ASSIGN_FIELD(ps.writes_stencil);
97   ASSIGN_FIELD(ps.writes_sample_mask);
98   ASSIGN_FIELD(ps.has_epilog);
99   ASSIGN_FIELD(ps.num_interp);
100   ASSIGN_FIELD(ps.spi_ps_input);
101   ASSIGN_FIELD(cs.subgroup_size);
102   ASSIGN_OUTINFO(ms);
103   radv_aco_convert_shader_so_info(aco_info, radv);
104   aco_info->gfx9_gs_ring_lds_size = radv->gs_ring_info.lds_size;
105}
106
107#define ASSIGN_VS_STATE_FIELD(x) aco_info->state.x = radv->state->x
108#define ASSIGN_VS_STATE_FIELD_CP(x) memcpy(&aco_info->state.x, &radv->state->x, sizeof(radv->state->x))
109static inline void
110radv_aco_convert_vs_prolog_key(struct aco_vs_prolog_key *aco_info,
111			       const struct radv_vs_prolog_key *radv)
112{
113   ASSIGN_VS_STATE_FIELD(instance_rate_inputs);
114   ASSIGN_VS_STATE_FIELD(nontrivial_divisors);
115   ASSIGN_VS_STATE_FIELD(post_shuffle);
116   ASSIGN_VS_STATE_FIELD(alpha_adjust_lo);
117   ASSIGN_VS_STATE_FIELD(alpha_adjust_hi);
118   ASSIGN_VS_STATE_FIELD_CP(divisors);
119   ASSIGN_VS_STATE_FIELD_CP(formats);
120   ASSIGN_FIELD(num_attributes);
121   ASSIGN_FIELD(misaligned_mask);
122   ASSIGN_FIELD(is_ngg);
123   ASSIGN_FIELD(next_stage);
124}
125
126static inline void
127radv_aco_convert_ps_epilog_key(struct aco_ps_epilog_key *aco_info,
128			       const struct radv_ps_epilog_key *radv)
129{
130   ASSIGN_FIELD(spi_shader_col_format);
131   ASSIGN_FIELD(color_is_int8);
132   ASSIGN_FIELD(color_is_int10);
133   ASSIGN_FIELD(enable_mrt_output_nan_fixup);
134}
135
136static inline void
137radv_aco_convert_pipe_key(struct aco_stage_input *aco_info,
138                          const struct radv_pipeline_key *radv)
139{
140   ASSIGN_FIELD(optimisations_disabled);
141   ASSIGN_FIELD(image_2d_view_of_3d);
142   ASSIGN_FIELD(vs.instance_rate_inputs);
143   ASSIGN_FIELD_CP(vs.instance_rate_divisors);
144   ASSIGN_FIELD_CP(vs.vertex_attribute_formats);
145   ASSIGN_FIELD_CP(vs.vertex_attribute_bindings);
146   ASSIGN_FIELD_CP(vs.vertex_attribute_offsets);
147   ASSIGN_FIELD_CP(vs.vertex_attribute_strides);
148   ASSIGN_FIELD_CP(vs.vertex_binding_align);
149   ASSIGN_FIELD(tcs.tess_input_vertices);
150   ASSIGN_FIELD(ps.col_format);
151   ASSIGN_FIELD(ps.num_samples);
152   ASSIGN_FIELD(ps.alpha_to_coverage_via_mrtz);
153}
154
155static inline void
156radv_aco_convert_opts(struct aco_compiler_options *aco_info,
157                      const struct radv_nir_compiler_options *radv)
158{
159   radv_aco_convert_pipe_key(&aco_info->key, &radv->key);
160   ASSIGN_FIELD(robust_buffer_access);
161   ASSIGN_FIELD(dump_shader);
162   ASSIGN_FIELD(dump_preoptir);
163   ASSIGN_FIELD(record_ir);
164   ASSIGN_FIELD(record_stats);
165   ASSIGN_FIELD(has_ls_vgpr_init_bug);
166   ASSIGN_FIELD(wgp_mode);
167   ASSIGN_FIELD(family);
168   ASSIGN_FIELD(gfx_level);
169   ASSIGN_FIELD(address32_hi);
170   ASSIGN_FIELD(debug.func);
171   ASSIGN_FIELD(debug.private_data);
172}
173#undef ASSIGN_VS_STATE_FIELD
174#undef ASSIGN_VS_STATE_FIELD_CP
175#undef ASSIGN_FIELD
176#undef ASSIGN_FIELD_CP
177#undef ASSIGN_OUTINFO
178
179#endif
180