radeonsi: move non-LLVM code out of si_shader_llvm.c

[mesa.git] / src / gallium / drivers / radeonsi / si_shader_internal.h

diff --git a/src/gallium/drivers/radeonsi/si_shader_internal.h b/src/gallium/drivers/radeonsi/si_shader_internal.h
index 6509edb81814c82c4eaee262958669778562997d..91b581294d2c81fb39eebf778122efc7929a0ef3 100644 (file)
--- a/src/gallium/drivers/radeonsi/si_shader_internal.h
+++ b/src/gallium/drivers/radeonsi/si_shader_internal.h
@@ -83,6 +83,7 @@ struct si_shader_context {
        /* Common inputs for merged shaders. */
        struct ac_arg merged_wave_info;
        struct ac_arg merged_scratch_offset;
+       struct ac_arg small_prim_cull_info;
        /* API VS */
        struct ac_arg vertex_buffers;
        struct ac_arg vb_descriptors[5];
@@ -95,6 +96,13 @@ struct si_shader_context {
         *   [2:3] = NGG: output primitive type
         *   [4:5] = NGG: provoking vertex index
         *   [6]   = NGG: streamout queries enabled
+        *   [7:10] = NGG: small prim filter precision = num_samples / quant_mode,
+        *            but in reality it's: 1/2^n, from 1/16 to 1/4096 = 1/2^4 to 1/2^12
+        *            Only the first 4 bits of the exponent are stored.
+        *            Set it like this: (fui(num_samples / quant_mode) >> 23)
+        *            Expand to FP32 like this: ((0x70 | value) << 23);
+        *            With 0x70 = 112, we get 2^(112 + value - 127) = 2^(value - 15)
+        *            = 1/2^(15 - value) in FP32
         *   [11:23] = stride between patches in DW = num_inputs * num_vertices * 4
         *             max = 32*32*4 + 32*4
         *   [24:31] = stride between vertices in DW = num_inputs * 4
@@ -102,6 +110,7 @@ struct si_shader_context {
         */
        struct ac_arg vs_state_bits;
        struct ac_arg vs_blit_inputs;
+       struct ac_arg ngg_old_thread_id; /* generated by the NGG cull shader */
        /* HW VS */
        struct ac_arg streamout_config;
        struct ac_arg streamout_write_index;
@@ -178,23 +187,6 @@ struct si_shader_context {
        LLVMValueRef gs_ngg_scratch;
        LLVMValueRef postponed_kill;
        LLVMValueRef return_value;
-
-       LLVMTypeRef voidt;
-       LLVMTypeRef i1;
-       LLVMTypeRef i8;
-       LLVMTypeRef i32;
-       LLVMTypeRef i64;
-       LLVMTypeRef i128;
-       LLVMTypeRef f32;
-       LLVMTypeRef v2i32;
-       LLVMTypeRef v4i32;
-       LLVMTypeRef v4f32;
-       LLVMTypeRef v8i32;
-
-       LLVMValueRef i32_0;
-       LLVMValueRef i32_1;
-       LLVMValueRef i1false;
-       LLVMValueRef i1true;
 };
 
 static inline struct si_shader_context *
@@ -208,9 +200,6 @@ void si_llvm_context_init(struct si_shader_context *ctx,
                          struct si_screen *sscreen,
                          struct ac_llvm_compiler *compiler,
                          unsigned wave_size);
-void si_llvm_context_set_ir(struct si_shader_context *ctx,
-                           struct si_shader *shader);
-
 void si_llvm_create_func(struct si_shader_context *ctx, const char *name,
                         LLVMTypeRef *return_types, unsigned num_return_elems,
                         unsigned max_workgroup_size);
@@ -297,12 +286,16 @@ void si_fix_resource_usage(struct si_screen *sscreen, struct si_shader *shader);
 void si_llvm_emit_streamout(struct si_shader_context *ctx,
                            struct si_shader_output_values *outputs,
                            unsigned noutput, unsigned stream);
-void si_create_function(struct si_shader_context *ctx);
+void si_create_function(struct si_shader_context *ctx, bool ngg_cull_shader);
 
 bool gfx10_ngg_export_prim_early(struct si_shader *shader);
 void gfx10_ngg_build_sendmsg_gs_alloc_req(struct si_shader_context *ctx);
 void gfx10_ngg_build_export_prim(struct si_shader_context *ctx,
-                                LLVMValueRef user_edgeflags[3]);
+                                LLVMValueRef user_edgeflags[3],
+                                LLVMValueRef prim_passthrough);
+void gfx10_emit_ngg_culling_epilogue_4x_wave32(struct ac_shader_abi *abi,
+                                              unsigned max_outputs,
+                                              LLVMValueRef *addrs);
 void gfx10_emit_ngg_epilogue(struct ac_shader_abi *abi,
                             unsigned max_outputs,
                             LLVMValueRef *addrs);