mirrors/gnss-sdr
1
0
Fork 0
mirror of https://github.com/gnss-sdr/gnss-sdr synced 2024-10-27 13:16:24 +00:00
Code Issues Releases Wiki Activity

Merge branch 'next' of https://github.com/gnss-sdr/gnss-sdr into next

Browse Source
This commit is contained in:
Carles Fernandez 2018-03-04 02:09:23 +01:00
commit 622786aed1
383 changed files with 8704 additions and 8229 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

7
src/algorithms/acquisition/gnuradio_blocks/galileo_pcps_8ms_acquisition_cc.cc
View File

@ -54,9 +54,10 @@ galileo_pcps_8ms_acquisition_cc::galileo_pcps_8ms_acquisition_cc(
unsigned int sampled_ms, unsigned int max_dwells, unsigned int sampled_ms, unsigned int max_dwells,
unsigned int doppler_max, long freq, long fs_in, unsigned int doppler_max, long freq, long fs_in,
int samples_per_ms, int samples_per_code, int samples_per_ms, int samples_per_code,
bool dump, std::string dump_filename) : gr::block("galileo_pcps_8ms_acquisition_cc", bool dump,
gr::io_signature::make(1, 1, sizeof(gr_complex) * sampled_ms * samples_per_ms), std::string dump_filename) : gr::block("galileo_pcps_8ms_acquisition_cc",
gr::io_signature::make(0, 0, sizeof(gr_complex) * sampled_ms * samples_per_ms)) gr::io_signature::make(1, 1, sizeof(gr_complex) * sampled_ms * samples_per_ms),
gr::io_signature::make(0, 0, sizeof(gr_complex) * sampled_ms * samples_per_ms))
{ {
this->message_port_register_out(pmt::mp("events")); this->message_port_register_out(pmt::mp("events"));
d_sample_counter = 0; // SAMPLE COUNTER d_sample_counter = 0; // SAMPLE COUNTER

4
src/algorithms/acquisition/gnuradio_blocks/gps_pcps_acquisition_fpga_sc.cc
View File

@ -71,9 +71,7 @@ gps_pcps_acquisition_fpga_sc::gps_pcps_acquisition_fpga_sc(
int samples_per_code, int vector_length, unsigned int nsamples_total, int samples_per_code, int vector_length, unsigned int nsamples_total,
bool bit_transition_flag, bool use_CFAR_algorithm_flag, bool bit_transition_flag, bool use_CFAR_algorithm_flag,
unsigned int select_queue_Fpga, std::string device_name, bool dump, unsigned int select_queue_Fpga, std::string device_name, bool dump,
std::string dump_filename) : std::string dump_filename) : gr::block("pcps_acquisition_fpga_sc",
gr::block("pcps_acquisition_fpga_sc",
gr::io_signature::make(0, 0, sizeof(lv_16sc_t)), gr::io_signature::make(0, 0, sizeof(lv_16sc_t)),
gr::io_signature::make(0, 0, 0)) gr::io_signature::make(0, 0, 0))
{ {

7
src/algorithms/acquisition/gnuradio_blocks/pcps_acquisition.cc
View File

@ -65,9 +65,10 @@ pcps_acquisition::pcps_acquisition(
int samples_per_ms, int samples_per_code, int samples_per_ms, int samples_per_code,
bool bit_transition_flag, bool use_CFAR_algorithm_flag, bool bit_transition_flag, bool use_CFAR_algorithm_flag,
bool dump, bool blocking, bool dump, bool blocking,
std::string dump_filename, size_t it_size) : gr::block("pcps_acquisition", std::string dump_filename,
gr::io_signature::make(1, 1, it_size * sampled_ms * samples_per_ms * (bit_transition_flag ? 2 : 1)), size_t it_size) : gr::block("pcps_acquisition",
gr::io_signature::make(0, 0, it_size * sampled_ms * samples_per_ms * (bit_transition_flag ? 2 : 1))) gr::io_signature::make(1, 1, it_size * sampled_ms * samples_per_ms * (bit_transition_flag ? 2 : 1)),
gr::io_signature::make(0, 0, it_size * sampled_ms * samples_per_ms * (bit_transition_flag ? 2 : 1)))
{ {
this->message_port_register_out(pmt::mp("events")); this->message_port_register_out(pmt::mp("events"));

7
src/algorithms/acquisition/gnuradio_blocks/pcps_cccwsr_acquisition_cc.cc
View File

@ -61,9 +61,10 @@ pcps_cccwsr_acquisition_cc::pcps_cccwsr_acquisition_cc(
unsigned int sampled_ms, unsigned int max_dwells, unsigned int sampled_ms, unsigned int max_dwells,
unsigned int doppler_max, long freq, long fs_in, unsigned int doppler_max, long freq, long fs_in,
int samples_per_ms, int samples_per_code, int samples_per_ms, int samples_per_code,
bool dump, std::string dump_filename) : gr::block("pcps_cccwsr_acquisition_cc", bool dump,
gr::io_signature::make(1, 1, sizeof(gr_complex) * sampled_ms * samples_per_ms), std::string dump_filename) : gr::block("pcps_cccwsr_acquisition_cc",
gr::io_signature::make(0, 0, sizeof(gr_complex) * sampled_ms * samples_per_ms)) gr::io_signature::make(1, 1, sizeof(gr_complex) * sampled_ms * samples_per_ms),
gr::io_signature::make(0, 0, sizeof(gr_complex) * sampled_ms * samples_per_ms))
{ {
this->message_port_register_out(pmt::mp("events")); this->message_port_register_out(pmt::mp("events"));
d_sample_counter = 0; // SAMPLE COUNTER d_sample_counter = 0; // SAMPLE COUNTER

7
src/algorithms/acquisition/gnuradio_blocks/pcps_quicksync_acquisition_cc.cc
View File

@ -67,9 +67,10 @@ pcps_quicksync_acquisition_cc::pcps_quicksync_acquisition_cc(
unsigned int doppler_max, long freq, long fs_in, unsigned int doppler_max, long freq, long fs_in,
int samples_per_ms, int samples_per_code, int samples_per_ms, int samples_per_code,
bool bit_transition_flag, bool bit_transition_flag,
bool dump, std::string dump_filename) : gr::block("pcps_quicksync_acquisition_cc", bool dump,
gr::io_signature::make(1, 1, (sizeof(gr_complex) * sampled_ms * samples_per_ms)), std::string dump_filename) : gr::block("pcps_quicksync_acquisition_cc",
gr::io_signature::make(0, 0, (sizeof(gr_complex) * sampled_ms * samples_per_ms))) gr::io_signature::make(1, 1, (sizeof(gr_complex) * sampled_ms * samples_per_ms)),
gr::io_signature::make(0, 0, (sizeof(gr_complex) * sampled_ms * samples_per_ms)))
{ {
this->message_port_register_out(pmt::mp("events")); this->message_port_register_out(pmt::mp("events"));
d_sample_counter = 0; // SAMPLE COUNTER d_sample_counter = 0; // SAMPLE COUNTER

7
src/algorithms/acquisition/gnuradio_blocks/pcps_tong_acquisition_cc.cc
View File

@ -76,9 +76,10 @@ pcps_tong_acquisition_cc::pcps_tong_acquisition_cc(
long freq, long fs_in, int samples_per_ms, long freq, long fs_in, int samples_per_ms,
int samples_per_code, unsigned int tong_init_val, int samples_per_code, unsigned int tong_init_val,
unsigned int tong_max_val, unsigned int tong_max_dwells, unsigned int tong_max_val, unsigned int tong_max_dwells,
bool dump, std::string dump_filename) : gr::block("pcps_tong_acquisition_cc", bool dump,
gr::io_signature::make(1, 1, sizeof(gr_complex) * sampled_ms * samples_per_ms), std::string dump_filename) : gr::block("pcps_tong_acquisition_cc",
gr::io_signature::make(0, 0, sizeof(gr_complex) * sampled_ms * samples_per_ms)) gr::io_signature::make(1, 1, sizeof(gr_complex) * sampled_ms * samples_per_ms),
gr::io_signature::make(0, 0, sizeof(gr_complex) * sampled_ms * samples_per_ms))
{ {
this->message_port_register_out(pmt::mp("events")); this->message_port_register_out(pmt::mp("events"));
d_sample_counter = 0; // SAMPLE COUNTER d_sample_counter = 0; // SAMPLE COUNTER

117
src/algorithms/libs/opencl/clFFT.h
View File

@ -50,85 +50,86 @@
#define __CLFFT_H #define __CLFFT_H
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
#include <stdio.h> #include <stdio.h>
#ifdef __APPLE__ #ifdef __APPLE__
#include <OpenCL/opencl.h> #include <OpenCL/opencl.h>
#else #else
#include <CL/cl.h> #include <CL/cl.h>
#endif #endif
// XForm type // XForm type
typedef enum typedef enum
{ {
clFFT_Forward = -1, clFFT_Forward = -1,
clFFT_Inverse = 1 clFFT_Inverse = 1
}clFFT_Direction;
// XForm dimension } clFFT_Direction;
typedef enum
{
clFFT_1D = 0,
clFFT_2D = 1,
clFFT_3D = 3
}clFFT_Dimension;
// XForm Data type // XForm dimension
typedef enum typedef enum
{ {
clFFT_SplitComplexFormat = 0, clFFT_1D = 0,
clFFT_InterleavedComplexFormat = 1 clFFT_2D = 1,
}clFFT_DataFormat; clFFT_3D = 3
typedef struct } clFFT_Dimension;
{
unsigned int x;
unsigned int y;
unsigned int z;
}clFFT_Dim3;
typedef struct
{
float *real;
float *imag;
} clFFT_SplitComplex;
typedef struct // XForm Data type
{ typedef enum
float real; {
float imag; clFFT_SplitComplexFormat = 0,
}clFFT_Complex; clFFT_InterleavedComplexFormat = 1
} clFFT_DataFormat;
typedef void* clFFT_Plan; typedef struct
{
unsigned int x;
unsigned int y;
unsigned int z;
} clFFT_Dim3;
clFFT_Plan clFFT_CreatePlan( cl_context context, clFFT_Dim3 n, clFFT_Dimension dim, clFFT_DataFormat dataFormat, cl_int *error_code ); typedef struct
{
float *real;
float *imag;
} clFFT_SplitComplex;
void clFFT_DestroyPlan( clFFT_Plan plan ); typedef struct
{
float real;
float imag;
} clFFT_Complex;
cl_int clFFT_ExecuteInterleaved( cl_command_queue queue, clFFT_Plan plan, cl_int batchSize, clFFT_Direction dir, typedef void *clFFT_Plan;
cl_mem data_in, cl_mem data_out,
cl_int num_events, cl_event *event_list, cl_event *event );
cl_int clFFT_ExecutePlannar( cl_command_queue queue, clFFT_Plan plan, cl_int batchSize, clFFT_Direction dir, clFFT_Plan clFFT_CreatePlan(cl_context context, clFFT_Dim3 n, clFFT_Dimension dim, clFFT_DataFormat dataFormat, cl_int *error_code);
cl_mem data_in_real, cl_mem data_in_imag, cl_mem data_out_real, cl_mem data_out_imag,
cl_int num_events, cl_event *event_list, cl_event *event );
cl_int clFFT_1DTwistInterleaved(clFFT_Plan Plan, cl_command_queue queue, cl_mem array, void clFFT_DestroyPlan(clFFT_Plan plan);
size_t numRows, size_t numCols, size_t startRow, size_t rowsToProcess, clFFT_Direction dir);
cl_int clFFT_1DTwistPlannar(clFFT_Plan Plan, cl_command_queue queue, cl_mem array_real, cl_mem array_imag, cl_int clFFT_ExecuteInterleaved(cl_command_queue queue, clFFT_Plan plan, cl_int batchSize, clFFT_Direction dir,
size_t numRows, size_t numCols, size_t startRow, size_t rowsToProcess, clFFT_Direction dir); cl_mem data_in, cl_mem data_out,
cl_int num_events, cl_event *event_list, cl_event *event);
void clFFT_DumpPlan( clFFT_Plan plan, FILE *file);
cl_int clFFT_ExecutePlannar(cl_command_queue queue, clFFT_Plan plan, cl_int batchSize, clFFT_Direction dir,
cl_mem data_in_real, cl_mem data_in_imag, cl_mem data_out_real, cl_mem data_out_imag,
cl_int num_events, cl_event *event_list, cl_event *event);
cl_int clFFT_1DTwistInterleaved(clFFT_Plan Plan, cl_command_queue queue, cl_mem array,
size_t numRows, size_t numCols, size_t startRow, size_t rowsToProcess, clFFT_Direction dir);
cl_int clFFT_1DTwistPlannar(clFFT_Plan Plan, cl_command_queue queue, cl_mem array_real, cl_mem array_imag,
size_t numRows, size_t numCols, size_t startRow, size_t rowsToProcess, clFFT_Direction dir);
void clFFT_DumpPlan(clFFT_Plan plan, FILE *file);
#ifdef __cplusplus #ifdef __cplusplus
} }
#endif #endif
#endif #endif

424
src/algorithms/libs/opencl/fft_base_kernels.h
View File

@ -54,224 +54,220 @@
using namespace std; using namespace std;
static string baseKernels = string( static string baseKernels = string(
"#ifndef M_PI\n" "#ifndef M_PI\n"
"#define M_PI 0x1.921fb54442d18p+1\n" "#define M_PI 0x1.921fb54442d18p+1\n"
"#endif\n" "#endif\n"
"#define complexMul(a,b) ((float2)(mad(-(a).y, (b).y, (a).x * (b).x), mad((a).y, (b).x, (a).x * (b).y)))\n" "#define complexMul(a,b) ((float2)(mad(-(a).y, (b).y, (a).x * (b).x), mad((a).y, (b).x, (a).x * (b).y)))\n"
"#define conj(a) ((float2)((a).x, -(a).y))\n" "#define conj(a) ((float2)((a).x, -(a).y))\n"
"#define conjTransp(a) ((float2)(-(a).y, (a).x))\n" "#define conjTransp(a) ((float2)(-(a).y, (a).x))\n"
"\n" "\n"
"#define fftKernel2(a,dir) \\\n" "#define fftKernel2(a,dir) \\\n"
"{ \\\n" "{ \\\n"
" float2 c = (a)[0]; \\\n" " float2 c = (a)[0]; \\\n"
" (a)[0] = c + (a)[1]; \\\n" " (a)[0] = c + (a)[1]; \\\n"
" (a)[1] = c - (a)[1]; \\\n" " (a)[1] = c - (a)[1]; \\\n"
"}\n" "}\n"
"\n" "\n"
"#define fftKernel2S(d1,d2,dir) \\\n" "#define fftKernel2S(d1,d2,dir) \\\n"
"{ \\\n" "{ \\\n"
" float2 c = (d1); \\\n" " float2 c = (d1); \\\n"
" (d1) = c + (d2); \\\n" " (d1) = c + (d2); \\\n"
" (d2) = c - (d2); \\\n" " (d2) = c - (d2); \\\n"
"}\n" "}\n"
"\n" "\n"
"#define fftKernel4(a,dir) \\\n" "#define fftKernel4(a,dir) \\\n"
"{ \\\n" "{ \\\n"
" fftKernel2S((a)[0], (a)[2], dir); \\\n" " fftKernel2S((a)[0], (a)[2], dir); \\\n"
" fftKernel2S((a)[1], (a)[3], dir); \\\n" " fftKernel2S((a)[1], (a)[3], dir); \\\n"
" fftKernel2S((a)[0], (a)[1], dir); \\\n" " fftKernel2S((a)[0], (a)[1], dir); \\\n"
" (a)[3] = (float2)(dir)*(conjTransp((a)[3])); \\\n" " (a)[3] = (float2)(dir)*(conjTransp((a)[3])); \\\n"
" fftKernel2S((a)[2], (a)[3], dir); \\\n" " fftKernel2S((a)[2], (a)[3], dir); \\\n"
" float2 c = (a)[1]; \\\n" " float2 c = (a)[1]; \\\n"
" (a)[1] = (a)[2]; \\\n" " (a)[1] = (a)[2]; \\\n"
" (a)[2] = c; \\\n" " (a)[2] = c; \\\n"
"}\n" "}\n"
"\n" "\n"
"#define fftKernel4s(a0,a1,a2,a3,dir) \\\n" "#define fftKernel4s(a0,a1,a2,a3,dir) \\\n"
"{ \\\n" "{ \\\n"
" fftKernel2S((a0), (a2), dir); \\\n" " fftKernel2S((a0), (a2), dir); \\\n"
" fftKernel2S((a1), (a3), dir); \\\n" " fftKernel2S((a1), (a3), dir); \\\n"
" fftKernel2S((a0), (a1), dir); \\\n" " fftKernel2S((a0), (a1), dir); \\\n"
" (a3) = (float2)(dir)*(conjTransp((a3))); \\\n" " (a3) = (float2)(dir)*(conjTransp((a3))); \\\n"
" fftKernel2S((a2), (a3), dir); \\\n" " fftKernel2S((a2), (a3), dir); \\\n"
" float2 c = (a1); \\\n" " float2 c = (a1); \\\n"
" (a1) = (a2); \\\n" " (a1) = (a2); \\\n"
" (a2) = c; \\\n" " (a2) = c; \\\n"
"}\n" "}\n"
"\n" "\n"
"#define bitreverse8(a) \\\n" "#define bitreverse8(a) \\\n"
"{ \\\n" "{ \\\n"
" float2 c; \\\n" " float2 c; \\\n"
" c = (a)[1]; \\\n" " c = (a)[1]; \\\n"
" (a)[1] = (a)[4]; \\\n" " (a)[1] = (a)[4]; \\\n"
" (a)[4] = c; \\\n" " (a)[4] = c; \\\n"
" c = (a)[3]; \\\n" " c = (a)[3]; \\\n"
" (a)[3] = (a)[6]; \\\n" " (a)[3] = (a)[6]; \\\n"
" (a)[6] = c; \\\n" " (a)[6] = c; \\\n"
"}\n" "}\n"
"\n" "\n"
"#define fftKernel8(a,dir) \\\n" "#define fftKernel8(a,dir) \\\n"
"{ \\\n" "{ \\\n"
" const float2 w1 = (float2)(0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f); \\\n" " const float2 w1 = (float2)(0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f); \\\n"
" const float2 w3 = (float2)(-0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f); \\\n" " const float2 w3 = (float2)(-0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f); \\\n"
" float2 c; \\\n" " float2 c; \\\n"
" fftKernel2S((a)[0], (a)[4], dir); \\\n" " fftKernel2S((a)[0], (a)[4], dir); \\\n"
" fftKernel2S((a)[1], (a)[5], dir); \\\n" " fftKernel2S((a)[1], (a)[5], dir); \\\n"
" fftKernel2S((a)[2], (a)[6], dir); \\\n" " fftKernel2S((a)[2], (a)[6], dir); \\\n"
" fftKernel2S((a)[3], (a)[7], dir); \\\n" " fftKernel2S((a)[3], (a)[7], dir); \\\n"
" (a)[5] = complexMul(w1, (a)[5]); \\\n" " (a)[5] = complexMul(w1, (a)[5]); \\\n"
" (a)[6] = (float2)(dir)*(conjTransp((a)[6])); \\\n" " (a)[6] = (float2)(dir)*(conjTransp((a)[6])); \\\n"
" (a)[7] = complexMul(w3, (a)[7]); \\\n" " (a)[7] = complexMul(w3, (a)[7]); \\\n"
" fftKernel2S((a)[0], (a)[2], dir); \\\n" " fftKernel2S((a)[0], (a)[2], dir); \\\n"
" fftKernel2S((a)[1], (a)[3], dir); \\\n" " fftKernel2S((a)[1], (a)[3], dir); \\\n"
" fftKernel2S((a)[4], (a)[6], dir); \\\n" " fftKernel2S((a)[4], (a)[6], dir); \\\n"
" fftKernel2S((a)[5], (a)[7], dir); \\\n" " fftKernel2S((a)[5], (a)[7], dir); \\\n"
" (a)[3] = (float2)(dir)*(conjTransp((a)[3])); \\\n" " (a)[3] = (float2)(dir)*(conjTransp((a)[3])); \\\n"
" (a)[7] = (float2)(dir)*(conjTransp((a)[7])); \\\n" " (a)[7] = (float2)(dir)*(conjTransp((a)[7])); \\\n"
" fftKernel2S((a)[0], (a)[1], dir); \\\n" " fftKernel2S((a)[0], (a)[1], dir); \\\n"
" fftKernel2S((a)[2], (a)[3], dir); \\\n" " fftKernel2S((a)[2], (a)[3], dir); \\\n"
" fftKernel2S((a)[4], (a)[5], dir); \\\n" " fftKernel2S((a)[4], (a)[5], dir); \\\n"
" fftKernel2S((a)[6], (a)[7], dir); \\\n" " fftKernel2S((a)[6], (a)[7], dir); \\\n"
" bitreverse8((a)); \\\n" " bitreverse8((a)); \\\n"
"}\n" "}\n"
"\n" "\n"
"#define bitreverse4x4(a) \\\n" "#define bitreverse4x4(a) \\\n"
"{ \\\n" "{ \\\n"
" float2 c; \\\n" " float2 c; \\\n"
" c = (a)[1]; (a)[1] = (a)[4]; (a)[4] = c; \\\n" " c = (a)[1]; (a)[1] = (a)[4]; (a)[4] = c; \\\n"
" c = (a)[2]; (a)[2] = (a)[8]; (a)[8] = c; \\\n" " c = (a)[2]; (a)[2] = (a)[8]; (a)[8] = c; \\\n"
" c = (a)[3]; (a)[3] = (a)[12]; (a)[12] = c; \\\n" " c = (a)[3]; (a)[3] = (a)[12]; (a)[12] = c; \\\n"
" c = (a)[6]; (a)[6] = (a)[9]; (a)[9] = c; \\\n" " c = (a)[6]; (a)[6] = (a)[9]; (a)[9] = c; \\\n"
" c = (a)[7]; (a)[7] = (a)[13]; (a)[13] = c; \\\n" " c = (a)[7]; (a)[7] = (a)[13]; (a)[13] = c; \\\n"
" c = (a)[11]; (a)[11] = (a)[14]; (a)[14] = c; \\\n" " c = (a)[11]; (a)[11] = (a)[14]; (a)[14] = c; \\\n"
"}\n" "}\n"
"\n" "\n"
"#define fftKernel16(a,dir) \\\n" "#define fftKernel16(a,dir) \\\n"
"{ \\\n" "{ \\\n"
" const float w0 = 0x1.d906bcp-1f; \\\n" " const float w0 = 0x1.d906bcp-1f; \\\n"
" const float w1 = 0x1.87de2ap-2f; \\\n" " const float w1 = 0x1.87de2ap-2f; \\\n"
" const float w2 = 0x1.6a09e6p-1f; \\\n" " const float w2 = 0x1.6a09e6p-1f; \\\n"
" fftKernel4s((a)[0], (a)[4], (a)[8], (a)[12], dir); \\\n" " fftKernel4s((a)[0], (a)[4], (a)[8], (a)[12], dir); \\\n"
" fftKernel4s((a)[1], (a)[5], (a)[9], (a)[13], dir); \\\n" " fftKernel4s((a)[1], (a)[5], (a)[9], (a)[13], dir); \\\n"
" fftKernel4s((a)[2], (a)[6], (a)[10], (a)[14], dir); \\\n" " fftKernel4s((a)[2], (a)[6], (a)[10], (a)[14], dir); \\\n"
" fftKernel4s((a)[3], (a)[7], (a)[11], (a)[15], dir); \\\n" " fftKernel4s((a)[3], (a)[7], (a)[11], (a)[15], dir); \\\n"
" (a)[5] = complexMul((a)[5], (float2)(w0, dir*w1)); \\\n" " (a)[5] = complexMul((a)[5], (float2)(w0, dir*w1)); \\\n"
" (a)[6] = complexMul((a)[6], (float2)(w2, dir*w2)); \\\n" " (a)[6] = complexMul((a)[6], (float2)(w2, dir*w2)); \\\n"
" (a)[7] = complexMul((a)[7], (float2)(w1, dir*w0)); \\\n" " (a)[7] = complexMul((a)[7], (float2)(w1, dir*w0)); \\\n"
" (a)[9] = complexMul((a)[9], (float2)(w2, dir*w2)); \\\n" " (a)[9] = complexMul((a)[9], (float2)(w2, dir*w2)); \\\n"
" (a)[10] = (float2)(dir)*(conjTransp((a)[10])); \\\n" " (a)[10] = (float2)(dir)*(conjTransp((a)[10])); \\\n"
" (a)[11] = complexMul((a)[11], (float2)(-w2, dir*w2)); \\\n" " (a)[11] = complexMul((a)[11], (float2)(-w2, dir*w2)); \\\n"
" (a)[13] = complexMul((a)[13], (float2)(w1, dir*w0)); \\\n" " (a)[13] = complexMul((a)[13], (float2)(w1, dir*w0)); \\\n"
" (a)[14] = complexMul((a)[14], (float2)(-w2, dir*w2)); \\\n" " (a)[14] = complexMul((a)[14], (float2)(-w2, dir*w2)); \\\n"
" (a)[15] = complexMul((a)[15], (float2)(-w0, dir*-w1)); \\\n" " (a)[15] = complexMul((a)[15], (float2)(-w0, dir*-w1)); \\\n"
" fftKernel4((a), dir); \\\n" " fftKernel4((a), dir); \\\n"
" fftKernel4((a) + 4, dir); \\\n" " fftKernel4((a) + 4, dir); \\\n"
" fftKernel4((a) + 8, dir); \\\n" " fftKernel4((a) + 8, dir); \\\n"
" fftKernel4((a) + 12, dir); \\\n" " fftKernel4((a) + 12, dir); \\\n"
" bitreverse4x4((a)); \\\n" " bitreverse4x4((a)); \\\n"
"}\n" "}\n"
"\n" "\n"
"#define bitreverse32(a) \\\n" "#define bitreverse32(a) \\\n"
"{ \\\n" "{ \\\n"
" float2 c1, c2; \\\n" " float2 c1, c2; \\\n"
" c1 = (a)[2]; (a)[2] = (a)[1]; c2 = (a)[4]; (a)[4] = c1; c1 = (a)[8]; (a)[8] = c2; c2 = (a)[16]; (a)[16] = c1; (a)[1] = c2; \\\n" " c1 = (a)[2]; (a)[2] = (a)[1]; c2 = (a)[4]; (a)[4] = c1; c1 = (a)[8]; (a)[8] = c2; c2 = (a)[16]; (a)[16] = c1; (a)[1] = c2; \\\n"
" c1 = (a)[6]; (a)[6] = (a)[3]; c2 = (a)[12]; (a)[12] = c1; c1 = (a)[24]; (a)[24] = c2; c2 = (a)[17]; (a)[17] = c1; (a)[3] = c2; \\\n" " c1 = (a)[6]; (a)[6] = (a)[3]; c2 = (a)[12]; (a)[12] = c1; c1 = (a)[24]; (a)[24] = c2; c2 = (a)[17]; (a)[17] = c1; (a)[3] = c2; \\\n"
" c1 = (a)[10]; (a)[10] = (a)[5]; c2 = (a)[20]; (a)[20] = c1; c1 = (a)[9]; (a)[9] = c2; c2 = (a)[18]; (a)[18] = c1; (a)[5] = c2; \\\n" " c1 = (a)[10]; (a)[10] = (a)[5]; c2 = (a)[20]; (a)[20] = c1; c1 = (a)[9]; (a)[9] = c2; c2 = (a)[18]; (a)[18] = c1; (a)[5] = c2; \\\n"
" c1 = (a)[14]; (a)[14] = (a)[7]; c2 = (a)[28]; (a)[28] = c1; c1 = (a)[25]; (a)[25] = c2; c2 = (a)[19]; (a)[19] = c1; (a)[7] = c2; \\\n" " c1 = (a)[14]; (a)[14] = (a)[7]; c2 = (a)[28]; (a)[28] = c1; c1 = (a)[25]; (a)[25] = c2; c2 = (a)[19]; (a)[19] = c1; (a)[7] = c2; \\\n"
" c1 = (a)[22]; (a)[22] = (a)[11]; c2 = (a)[13]; (a)[13] = c1; c1 = (a)[26]; (a)[26] = c2; c2 = (a)[21]; (a)[21] = c1; (a)[11] = c2; \\\n" " c1 = (a)[22]; (a)[22] = (a)[11]; c2 = (a)[13]; (a)[13] = c1; c1 = (a)[26]; (a)[26] = c2; c2 = (a)[21]; (a)[21] = c1; (a)[11] = c2; \\\n"
" c1 = (a)[30]; (a)[30] = (a)[15]; c2 = (a)[29]; (a)[29] = c1; c1 = (a)[27]; (a)[27] = c2; c2 = (a)[23]; (a)[23] = c1; (a)[15] = c2; \\\n" " c1 = (a)[30]; (a)[30] = (a)[15]; c2 = (a)[29]; (a)[29] = c1; c1 = (a)[27]; (a)[27] = c2; c2 = (a)[23]; (a)[23] = c1; (a)[15] = c2; \\\n"
"}\n" "}\n"
"\n" "\n"
"#define fftKernel32(a,dir) \\\n" "#define fftKernel32(a,dir) \\\n"
"{ \\\n" "{ \\\n"
" fftKernel2S((a)[0], (a)[16], dir); \\\n" " fftKernel2S((a)[0], (a)[16], dir); \\\n"
" fftKernel2S((a)[1], (a)[17], dir); \\\n" " fftKernel2S((a)[1], (a)[17], dir); \\\n"
" fftKernel2S((a)[2], (a)[18], dir); \\\n" " fftKernel2S((a)[2], (a)[18], dir); \\\n"
" fftKernel2S((a)[3], (a)[19], dir); \\\n" " fftKernel2S((a)[3], (a)[19], dir); \\\n"
" fftKernel2S((a)[4], (a)[20], dir); \\\n" " fftKernel2S((a)[4], (a)[20], dir); \\\n"
" fftKernel2S((a)[5], (a)[21], dir); \\\n" " fftKernel2S((a)[5], (a)[21], dir); \\\n"
" fftKernel2S((a)[6], (a)[22], dir); \\\n" " fftKernel2S((a)[6], (a)[22], dir); \\\n"
" fftKernel2S((a)[7], (a)[23], dir); \\\n" " fftKernel2S((a)[7], (a)[23], dir); \\\n"
" fftKernel2S((a)[8], (a)[24], dir); \\\n" " fftKernel2S((a)[8], (a)[24], dir); \\\n"
" fftKernel2S((a)[9], (a)[25], dir); \\\n" " fftKernel2S((a)[9], (a)[25], dir); \\\n"
" fftKernel2S((a)[10], (a)[26], dir); \\\n" " fftKernel2S((a)[10], (a)[26], dir); \\\n"
" fftKernel2S((a)[11], (a)[27], dir); \\\n" " fftKernel2S((a)[11], (a)[27], dir); \\\n"
" fftKernel2S((a)[12], (a)[28], dir); \\\n" " fftKernel2S((a)[12], (a)[28], dir); \\\n"
" fftKernel2S((a)[13], (a)[29], dir); \\\n" " fftKernel2S((a)[13], (a)[29], dir); \\\n"
" fftKernel2S((a)[14], (a)[30], dir); \\\n" " fftKernel2S((a)[14], (a)[30], dir); \\\n"
" fftKernel2S((a)[15], (a)[31], dir); \\\n" " fftKernel2S((a)[15], (a)[31], dir); \\\n"
" (a)[17] = complexMul((a)[17], (float2)(0x1.f6297cp-1f, dir*0x1.8f8b84p-3f)); \\\n" " (a)[17] = complexMul((a)[17], (float2)(0x1.f6297cp-1f, dir*0x1.8f8b84p-3f)); \\\n"
" (a)[18] = complexMul((a)[18], (float2)(0x1.d906bcp-1f, dir*0x1.87de2ap-2f)); \\\n" " (a)[18] = complexMul((a)[18], (float2)(0x1.d906bcp-1f, dir*0x1.87de2ap-2f)); \\\n"
" (a)[19] = complexMul((a)[19], (float2)(0x1.a9b662p-1f, dir*0x1.1c73b4p-1f)); \\\n" " (a)[19] = complexMul((a)[19], (float2)(0x1.a9b662p-1f, dir*0x1.1c73b4p-1f)); \\\n"
" (a)[20] = complexMul((a)[20], (float2)(0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f)); \\\n" " (a)[20] = complexMul((a)[20], (float2)(0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f)); \\\n"
" (a)[21] = complexMul((a)[21], (float2)(0x1.1c73b4p-1f, dir*0x1.a9b662p-1f)); \\\n" " (a)[21] = complexMul((a)[21], (float2)(0x1.1c73b4p-1f, dir*0x1.a9b662p-1f)); \\\n"
" (a)[22] = complexMul((a)[22], (float2)(0x1.87de2ap-2f, dir*0x1.d906bcp-1f)); \\\n" " (a)[22] = complexMul((a)[22], (float2)(0x1.87de2ap-2f, dir*0x1.d906bcp-1f)); \\\n"
" (a)[23] = complexMul((a)[23], (float2)(0x1.8f8b84p-3f, dir*0x1.f6297cp-1f)); \\\n" " (a)[23] = complexMul((a)[23], (float2)(0x1.8f8b84p-3f, dir*0x1.f6297cp-1f)); \\\n"
" (a)[24] = complexMul((a)[24], (float2)(0x0p+0f, dir*0x1p+0f)); \\\n" " (a)[24] = complexMul((a)[24], (float2)(0x0p+0f, dir*0x1p+0f)); \\\n"
" (a)[25] = complexMul((a)[25], (float2)(-0x1.8f8b84p-3f, dir*0x1.f6297cp-1f)); \\\n" " (a)[25] = complexMul((a)[25], (float2)(-0x1.8f8b84p-3f, dir*0x1.f6297cp-1f)); \\\n"
" (a)[26] = complexMul((a)[26], (float2)(-0x1.87de2ap-2f, dir*0x1.d906bcp-1f)); \\\n" " (a)[26] = complexMul((a)[26], (float2)(-0x1.87de2ap-2f, dir*0x1.d906bcp-1f)); \\\n"
" (a)[27] = complexMul((a)[27], (float2)(-0x1.1c73b4p-1f, dir*0x1.a9b662p-1f)); \\\n" " (a)[27] = complexMul((a)[27], (float2)(-0x1.1c73b4p-1f, dir*0x1.a9b662p-1f)); \\\n"
" (a)[28] = complexMul((a)[28], (float2)(-0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f)); \\\n" " (a)[28] = complexMul((a)[28], (float2)(-0x1.6a09e6p-1f, dir*0x1.6a09e6p-1f)); \\\n"
" (a)[29] = complexMul((a)[29], (float2)(-0x1.a9b662p-1f, dir*0x1.1c73b4p-1f)); \\\n" " (a)[29] = complexMul((a)[29], (float2)(-0x1.a9b662p-1f, dir*0x1.1c73b4p-1f)); \\\n"
" (a)[30] = complexMul((a)[30], (float2)(-0x1.d906bcp-1f, dir*0x1.87de2ap-2f)); \\\n" " (a)[30] = complexMul((a)[30], (float2)(-0x1.d906bcp-1f, dir*0x1.87de2ap-2f)); \\\n"
" (a)[31] = complexMul((a)[31], (float2)(-0x1.f6297cp-1f, dir*0x1.8f8b84p-3f)); \\\n" " (a)[31] = complexMul((a)[31], (float2)(-0x1.f6297cp-1f, dir*0x1.8f8b84p-3f)); \\\n"
" fftKernel16((a), dir); \\\n" " fftKernel16((a), dir); \\\n"
" fftKernel16((a) + 16, dir); \\\n" " fftKernel16((a) + 16, dir); \\\n"
" bitreverse32((a)); \\\n" " bitreverse32((a)); \\\n"
"}\n\n" "}\n\n");
);
static string twistKernelInterleaved = string( static string twistKernelInterleaved = string(
"__kernel void \\\n" "__kernel void \\\n"
"clFFT_1DTwistInterleaved(__global float2 *in, unsigned int startRow, unsigned int numCols, unsigned int N, unsigned int numRowsToProcess, int dir) \\\n" "clFFT_1DTwistInterleaved(__global float2 *in, unsigned int startRow, unsigned int numCols, unsigned int N, unsigned int numRowsToProcess, int dir) \\\n"
"{ \\\n" "{ \\\n"
" float2 a, w; \\\n" " float2 a, w; \\\n"
" float ang; \\\n" " float ang; \\\n"
" unsigned int j; \\\n" " unsigned int j; \\\n"
" unsigned int i = get_global_id(0); \\\n" " unsigned int i = get_global_id(0); \\\n"
" unsigned int startIndex = i; \\\n" " unsigned int startIndex = i; \\\n"
" \\\n" " \\\n"
" if(i < numCols) \\\n" " if(i < numCols) \\\n"
" { \\\n" " { \\\n"
" for(j = 0; j < numRowsToProcess; j++) \\\n" " for(j = 0; j < numRowsToProcess; j++) \\\n"
" { \\\n" " { \\\n"
" a = in[startIndex]; \\\n" " a = in[startIndex]; \\\n"
" ang = 2.0f * M_PI * dir * i * (startRow + j) / N; \\\n" " ang = 2.0f * M_PI * dir * i * (startRow + j) / N; \\\n"
" w = (float2)(native_cos(ang), native_sin(ang)); \\\n" " w = (float2)(native_cos(ang), native_sin(ang)); \\\n"
" a = complexMul(a, w); \\\n" " a = complexMul(a, w); \\\n"
" in[startIndex] = a; \\\n" " in[startIndex] = a; \\\n"
" startIndex += numCols; \\\n" " startIndex += numCols; \\\n"
" } \\\n" " } \\\n"
" } \\\n" " } \\\n"
"} \\\n" "} \\\n");
);
static string twistKernelPlannar = string( static string twistKernelPlannar = string(
"__kernel void \\\n" "__kernel void \\\n"
"clFFT_1DTwistSplit(__global float *in_real, __global float *in_imag , unsigned int startRow, unsigned int numCols, unsigned int N, unsigned int numRowsToProcess, int dir) \\\n" "clFFT_1DTwistSplit(__global float *in_real, __global float *in_imag , unsigned int startRow, unsigned int numCols, unsigned int N, unsigned int numRowsToProcess, int dir) \\\n"
"{ \\\n" "{ \\\n"
" float2 a, w; \\\n" " float2 a, w; \\\n"
" float ang; \\\n" " float ang; \\\n"
" unsigned int j; \\\n" " unsigned int j; \\\n"
" unsigned int i = get_global_id(0); \\\n" " unsigned int i = get_global_id(0); \\\n"
" unsigned int startIndex = i; \\\n" " unsigned int startIndex = i; \\\n"
" \\\n" " \\\n"
" if(i < numCols) \\\n" " if(i < numCols) \\\n"
" { \\\n" " { \\\n"
" for(j = 0; j < numRowsToProcess; j++) \\\n" " for(j = 0; j < numRowsToProcess; j++) \\\n"
" { \\\n" " { \\\n"
" a = (float2)(in_real[startIndex], in_imag[startIndex]); \\\n" " a = (float2)(in_real[startIndex], in_imag[startIndex]); \\\n"
" ang = 2.0f * M_PI * dir * i * (startRow + j) / N; \\\n" " ang = 2.0f * M_PI * dir * i * (startRow + j) / N; \\\n"
" w = (float2)(native_cos(ang), native_sin(ang)); \\\n" " w = (float2)(native_cos(ang), native_sin(ang)); \\\n"
" a = complexMul(a, w); \\\n" " a = complexMul(a, w); \\\n"
" in_real[startIndex] = a.x; \\\n" " in_real[startIndex] = a.x; \\\n"
" in_imag[startIndex] = a.y; \\\n" " in_imag[startIndex] = a.y; \\\n"
" startIndex += numCols; \\\n" " startIndex += numCols; \\\n"
" } \\\n" " } \\\n"
" } \\\n" " } \\\n"
"} \\\n" "} \\\n");
);
#endif #endif

652
src/algorithms/libs/opencl/fft_execute.cc
View File

@ -52,354 +52,352 @@
#include <stdio.h> #include <stdio.h>
#include <math.h> #include <math.h>
#define max(a,b) (((a)>(b)) ? (a) : (b)) #define max(a, b) (((a) > (b)) ? (a) : (b))
#define min(a,b) (((a)<(b)) ? (a) : (b)) #define min(a, b) (((a) < (b)) ? (a) : (b))
static cl_int static cl_int
allocateTemporaryBufferInterleaved(cl_fft_plan *plan, cl_uint batchSize) allocateTemporaryBufferInterleaved(cl_fft_plan *plan, cl_uint batchSize)
{ {
cl_int err = CL_SUCCESS; cl_int err = CL_SUCCESS;
if(plan->temp_buffer_needed && plan->last_batch_size != batchSize) if (plan->temp_buffer_needed && plan->last_batch_size != batchSize)
{ {
plan->last_batch_size = batchSize; plan->last_batch_size = batchSize;
size_t tmpLength = plan->n.x * plan->n.y * plan->n.z * batchSize * 2 * sizeof(cl_float); size_t tmpLength = plan->n.x * plan->n.y * plan->n.z * batchSize * 2 * sizeof(cl_float);
if(plan->tempmemobj) if (plan->tempmemobj)
clReleaseMemObject(plan->tempmemobj); clReleaseMemObject(plan->tempmemobj);
plan->tempmemobj = clCreateBuffer(plan->context, CL_MEM_READ_WRITE, tmpLength, NULL, &err); plan->tempmemobj = clCreateBuffer(plan->context, CL_MEM_READ_WRITE, tmpLength, NULL, &err);
} }
return err; return err;
} }
static cl_int static cl_int
allocateTemporaryBufferPlannar(cl_fft_plan *plan, cl_uint batchSize) allocateTemporaryBufferPlannar(cl_fft_plan *plan, cl_uint batchSize)
{ {
cl_int err = CL_SUCCESS; cl_int err = CL_SUCCESS;
cl_int terr; cl_int terr;
if(plan->temp_buffer_needed && plan->last_batch_size != batchSize) if (plan->temp_buffer_needed && plan->last_batch_size != batchSize)
{ {
plan->last_batch_size = batchSize; plan->last_batch_size = batchSize;
size_t tmpLength = plan->n.x * plan->n.y * plan->n.z * batchSize * sizeof(cl_float); size_t tmpLength = plan->n.x * plan->n.y * plan->n.z * batchSize * sizeof(cl_float);
if(plan->tempmemobj_real)
clReleaseMemObject(plan->tempmemobj_real);
if(plan->tempmemobj_imag) if (plan->tempmemobj_real)
clReleaseMemObject(plan->tempmemobj_imag); clReleaseMemObject(plan->tempmemobj_real);
plan->tempmemobj_real = clCreateBuffer(plan->context, CL_MEM_READ_WRITE, tmpLength, NULL, &err); if (plan->tempmemobj_imag)
plan->tempmemobj_imag = clCreateBuffer(plan->context, CL_MEM_READ_WRITE, tmpLength, NULL, &terr); clReleaseMemObject(plan->tempmemobj_imag);
err |= terr;
} plan->tempmemobj_real = clCreateBuffer(plan->context, CL_MEM_READ_WRITE, tmpLength, NULL, &err);
return err; plan->tempmemobj_imag = clCreateBuffer(plan->context, CL_MEM_READ_WRITE, tmpLength, NULL, &terr);
err |= terr;
}
return err;
} }
void void getKernelWorkDimensions(cl_fft_plan *plan, cl_fft_kernel_info *kernelInfo, cl_int *batchSize, size_t *gWorkItems, size_t *lWorkItems)
getKernelWorkDimensions(cl_fft_plan *plan, cl_fft_kernel_info *kernelInfo, cl_int *batchSize, size_t *gWorkItems, size_t *lWorkItems)
{ {
*lWorkItems = kernelInfo->num_workitems_per_workgroup; *lWorkItems = kernelInfo->num_workitems_per_workgroup;
int numWorkGroups = kernelInfo->num_workgroups; int numWorkGroups = kernelInfo->num_workgroups;
int numXFormsPerWG = kernelInfo->num_xforms_per_workgroup; int numXFormsPerWG = kernelInfo->num_xforms_per_workgroup;
switch(kernelInfo->dir) switch (kernelInfo->dir)
{ {
case cl_fft_kernel_x: case cl_fft_kernel_x:
*batchSize *= (plan->n.y * plan->n.z); *batchSize *= (plan->n.y * plan->n.z);
numWorkGroups = (*batchSize % numXFormsPerWG) ? (*batchSize/numXFormsPerWG + 1) : (*batchSize/numXFormsPerWG); numWorkGroups = (*batchSize % numXFormsPerWG) ? (*batchSize / numXFormsPerWG + 1) : (*batchSize / numXFormsPerWG);
numWorkGroups *= kernelInfo->num_workgroups; numWorkGroups *= kernelInfo->num_workgroups;
break; break;
case cl_fft_kernel_y: case cl_fft_kernel_y:
*batchSize *= plan->n.z; *batchSize *= plan->n.z;
numWorkGroups *= *batchSize; numWorkGroups *= *batchSize;
break; break;
case cl_fft_kernel_z: case cl_fft_kernel_z:
numWorkGroups *= *batchSize; numWorkGroups *= *batchSize;
break; break;
} }
*gWorkItems = numWorkGroups * *lWorkItems; *gWorkItems = numWorkGroups * *lWorkItems;
} }
cl_int cl_int
clFFT_ExecuteInterleaved( cl_command_queue queue, clFFT_Plan Plan, cl_int batchSize, clFFT_Direction dir, clFFT_ExecuteInterleaved(cl_command_queue queue, clFFT_Plan Plan, cl_int batchSize, clFFT_Direction dir,
cl_mem data_in, cl_mem data_out, cl_mem data_in, cl_mem data_out,
cl_int num_events, cl_event *event_list, cl_event *event ) cl_int num_events, cl_event *event_list, cl_event *event)
{
int s;
cl_fft_plan *plan = (cl_fft_plan *) Plan;
if(plan->format != clFFT_InterleavedComplexFormat)
return CL_INVALID_VALUE;
cl_int err;
size_t gWorkItems, lWorkItems;
int inPlaceDone;
cl_int isInPlace = data_in == data_out ? 1 : 0;
if((err = allocateTemporaryBufferInterleaved(plan, batchSize)) != CL_SUCCESS)
return err;
cl_mem memObj[3];
memObj[0] = data_in;
memObj[1] = data_out;
memObj[2] = plan->tempmemobj;
cl_fft_kernel_info *kernelInfo = plan->kernel_info;
int numKernels = plan->num_kernels;
int numKernelsOdd = numKernels & 1;
int currRead = 0;
int currWrite = 1;
// at least one external dram shuffle (transpose) required
if(plan->temp_buffer_needed)
{
// in-place transform
if(isInPlace)
{
inPlaceDone = 0;
currRead = 1;
currWrite = 2;
}
else
{
currWrite = (numKernels & 1) ? 1 : 2;
}
while(kernelInfo)
{
if( isInPlace && numKernelsOdd && !inPlaceDone && kernelInfo->in_place_possible)
{
currWrite = currRead;
inPlaceDone = 1;
}
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if(err)
return err;
currRead = (currWrite == 1) ? 1 : 2;
currWrite = (currWrite == 1) ? 2 : 1;
kernelInfo = kernelInfo->next;
}
}
// no dram shuffle (transpose required) transform
// all kernels can execute in-place.
else {
while(kernelInfo)
{
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if(err)
return err;
currRead = 1;
currWrite = 1;
kernelInfo = kernelInfo->next;
}
}
return err;
}
cl_int
clFFT_ExecutePlannar( cl_command_queue queue, clFFT_Plan Plan, cl_int batchSize, clFFT_Direction dir,
cl_mem data_in_real, cl_mem data_in_imag, cl_mem data_out_real, cl_mem data_out_imag,
cl_int num_events, cl_event *event_list, cl_event *event)
{
int s;
cl_fft_plan *plan = (cl_fft_plan *) Plan;
if(plan->format != clFFT_SplitComplexFormat)
return CL_INVALID_VALUE;
cl_int err;
size_t gWorkItems, lWorkItems;
int inPlaceDone;
cl_int isInPlace = ((data_in_real == data_out_real) && (data_in_imag == data_out_imag)) ? 1 : 0;
if((err = allocateTemporaryBufferPlannar(plan, batchSize)) != CL_SUCCESS)
return err;
cl_mem memObj_real[3];
cl_mem memObj_imag[3];
memObj_real[0] = data_in_real;
memObj_real[1] = data_out_real;
memObj_real[2] = plan->tempmemobj_real;
memObj_imag[0] = data_in_imag;
memObj_imag[1] = data_out_imag;
memObj_imag[2] = plan->tempmemobj_imag;
cl_fft_kernel_info *kernelInfo = plan->kernel_info;
int numKernels = plan->num_kernels;
int numKernelsOdd = numKernels & 1;
int currRead = 0;
int currWrite = 1;
// at least one external dram shuffle (transpose) required
if(plan->temp_buffer_needed)
{
// in-place transform
if(isInPlace)
{
inPlaceDone = 0;
currRead = 1;
currWrite = 2;
}
else
{
currWrite = (numKernels & 1) ? 1 : 2;
}
while(kernelInfo)
{
if( isInPlace && numKernelsOdd && !inPlaceDone && kernelInfo->in_place_possible)
{
currWrite = currRead;
inPlaceDone = 1;
}
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj_real[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj_imag[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_mem), &memObj_real[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_mem), &memObj_imag[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 4, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 5, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if(err)
return err;
currRead = (currWrite == 1) ? 1 : 2;
currWrite = (currWrite == 1) ? 2 : 1;
kernelInfo = kernelInfo->next;
}
}
// no dram shuffle (transpose required) transform
else {
while(kernelInfo)
{
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj_real[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj_imag[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_mem), &memObj_real[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_mem), &memObj_imag[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 4, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 5, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if(err)
return err;
currRead = 1;
currWrite = 1;
kernelInfo = kernelInfo->next;
}
}
return err;
}
cl_int
clFFT_1DTwistInterleaved(clFFT_Plan Plan, cl_command_queue queue, cl_mem array,
unsigned numRows, unsigned numCols, unsigned startRow, unsigned rowsToProcess, clFFT_Direction dir)
{ {
cl_fft_plan *plan = (cl_fft_plan *) Plan; int s;
cl_fft_plan *plan = (cl_fft_plan *)Plan;
unsigned int N = numRows*numCols; if (plan->format != clFFT_InterleavedComplexFormat)
unsigned int nCols = numCols; return CL_INVALID_VALUE;
unsigned int sRow = startRow;
unsigned int rToProcess = rowsToProcess; cl_int err;
int d = dir; size_t gWorkItems, lWorkItems;
int err = 0; int inPlaceDone;
cl_device_id device_id; cl_int isInPlace = data_in == data_out ? 1 : 0;
err = clGetCommandQueueInfo(queue, CL_QUEUE_DEVICE, sizeof(cl_device_id), &device_id, NULL);
if(err) if ((err = allocateTemporaryBufferInterleaved(plan, batchSize)) != CL_SUCCESS)
return err; return err;
size_t gSize; cl_mem memObj[3];
err = clGetKernelWorkGroupInfo(plan->twist_kernel, device_id, CL_KERNEL_WORK_GROUP_SIZE, sizeof(size_t), &gSize, NULL); memObj[0] = data_in;
if(err) memObj[1] = data_out;
return err; memObj[2] = plan->tempmemobj;
cl_fft_kernel_info *kernelInfo = plan->kernel_info;
gSize = min(128, gSize); int numKernels = plan->num_kernels;
size_t numGlobalThreads[1] = { max(numCols / gSize, 1)*gSize };
size_t numLocalThreads[1] = { gSize }; int numKernelsOdd = numKernels & 1;
int currRead = 0;
err |= clSetKernelArg(plan->twist_kernel, 0, sizeof(cl_mem), &array); int currWrite = 1;
err |= clSetKernelArg(plan->twist_kernel, 1, sizeof(unsigned int), &sRow);
err |= clSetKernelArg(plan->twist_kernel, 2, sizeof(unsigned int), &nCols); // at least one external dram shuffle (transpose) required
err |= clSetKernelArg(plan->twist_kernel, 3, sizeof(unsigned int), &N); if (plan->temp_buffer_needed)
err |= clSetKernelArg(plan->twist_kernel, 4, sizeof(unsigned int), &rToProcess); {
err |= clSetKernelArg(plan->twist_kernel, 5, sizeof(int), &d); // in-place transform
if (isInPlace)
err |= clEnqueueNDRangeKernel(queue, plan->twist_kernel, 1, NULL, numGlobalThreads, numLocalThreads, 0, NULL, NULL); {
inPlaceDone = 0;
return err; currRead = 1;
currWrite = 2;
}
else
{
currWrite = (numKernels & 1) ? 1 : 2;
}
while (kernelInfo)
{
if (isInPlace && numKernelsOdd && !inPlaceDone && kernelInfo->in_place_possible)
{
currWrite = currRead;
inPlaceDone = 1;
}
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if (err)
return err;
currRead = (currWrite == 1) ? 1 : 2;
currWrite = (currWrite == 1) ? 2 : 1;
kernelInfo = kernelInfo->next;
}
}
// no dram shuffle (transpose required) transform
// all kernels can execute in-place.
else
{
while (kernelInfo)
{
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if (err)
return err;
currRead = 1;
currWrite = 1;
kernelInfo = kernelInfo->next;
}
}
return err;
} }
cl_int cl_int
clFFT_1DTwistPlannar(clFFT_Plan Plan, cl_command_queue queue, cl_mem array_real, cl_mem array_imag, clFFT_ExecutePlannar(cl_command_queue queue, clFFT_Plan Plan, cl_int batchSize, clFFT_Direction dir,
unsigned numRows, unsigned numCols, unsigned startRow, unsigned rowsToProcess, clFFT_Direction dir) cl_mem data_in_real, cl_mem data_in_imag, cl_mem data_out_real, cl_mem data_out_imag,
cl_int num_events, cl_event *event_list, cl_event *event)
{ {
cl_fft_plan *plan = (cl_fft_plan *) Plan; int s;
cl_fft_plan *plan = (cl_fft_plan *)Plan;
unsigned int N = numRows*numCols;
unsigned int nCols = numCols; if (plan->format != clFFT_SplitComplexFormat)
unsigned int sRow = startRow; return CL_INVALID_VALUE;
unsigned int rToProcess = rowsToProcess;
int d = dir; cl_int err;
int err = 0; size_t gWorkItems, lWorkItems;
int inPlaceDone;
cl_device_id device_id;
err = clGetCommandQueueInfo(queue, CL_QUEUE_DEVICE, sizeof(cl_device_id), &device_id, NULL); cl_int isInPlace = ((data_in_real == data_out_real) && (data_in_imag == data_out_imag)) ? 1 : 0;
if(err)
return err; if ((err = allocateTemporaryBufferPlannar(plan, batchSize)) != CL_SUCCESS)
return err;
size_t gSize;
err = clGetKernelWorkGroupInfo(plan->twist_kernel, device_id, CL_KERNEL_WORK_GROUP_SIZE, sizeof(size_t), &gSize, NULL); cl_mem memObj_real[3];
if(err) cl_mem memObj_imag[3];
return err; memObj_real[0] = data_in_real;
memObj_real[1] = data_out_real;
gSize = min(128, gSize); memObj_real[2] = plan->tempmemobj_real;
size_t numGlobalThreads[1] = { max(numCols / gSize, 1)*gSize }; memObj_imag[0] = data_in_imag;
size_t numLocalThreads[1] = { gSize }; memObj_imag[1] = data_out_imag;
memObj_imag[2] = plan->tempmemobj_imag;
err |= clSetKernelArg(plan->twist_kernel, 0, sizeof(cl_mem), &array_real);
err |= clSetKernelArg(plan->twist_kernel, 1, sizeof(cl_mem), &array_imag); cl_fft_kernel_info *kernelInfo = plan->kernel_info;
err |= clSetKernelArg(plan->twist_kernel, 2, sizeof(unsigned int), &sRow); int numKernels = plan->num_kernels;
err |= clSetKernelArg(plan->twist_kernel, 3, sizeof(unsigned int), &nCols);
err |= clSetKernelArg(plan->twist_kernel, 4, sizeof(unsigned int), &N); int numKernelsOdd = numKernels & 1;
err |= clSetKernelArg(plan->twist_kernel, 5, sizeof(unsigned int), &rToProcess); int currRead = 0;
err |= clSetKernelArg(plan->twist_kernel, 6, sizeof(int), &d); int currWrite = 1;
err |= clEnqueueNDRangeKernel(queue, plan->twist_kernel, 1, NULL, numGlobalThreads, numLocalThreads, 0, NULL, NULL); // at least one external dram shuffle (transpose) required
if (plan->temp_buffer_needed)
return err; {
// in-place transform
if (isInPlace)
{
inPlaceDone = 0;
currRead = 1;
currWrite = 2;
}
else
{
currWrite = (numKernels & 1) ? 1 : 2;
}
while (kernelInfo)
{
if (isInPlace && numKernelsOdd && !inPlaceDone && kernelInfo->in_place_possible)
{
currWrite = currRead;
inPlaceDone = 1;
}
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj_real[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj_imag[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_mem), &memObj_real[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_mem), &memObj_imag[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 4, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 5, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if (err)
return err;
currRead = (currWrite == 1) ? 1 : 2;
currWrite = (currWrite == 1) ? 2 : 1;
kernelInfo = kernelInfo->next;
}
}
// no dram shuffle (transpose required) transform
else
{
while (kernelInfo)
{
s = batchSize;
getKernelWorkDimensions(plan, kernelInfo, &s, &gWorkItems, &lWorkItems);
err |= clSetKernelArg(kernelInfo->kernel, 0, sizeof(cl_mem), &memObj_real[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 1, sizeof(cl_mem), &memObj_imag[currRead]);
err |= clSetKernelArg(kernelInfo->kernel, 2, sizeof(cl_mem), &memObj_real[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 3, sizeof(cl_mem), &memObj_imag[currWrite]);
err |= clSetKernelArg(kernelInfo->kernel, 4, sizeof(cl_int), &dir);
err |= clSetKernelArg(kernelInfo->kernel, 5, sizeof(cl_int), &s);
err |= clEnqueueNDRangeKernel(queue, kernelInfo->kernel, 1, NULL, &gWorkItems, &lWorkItems, 0, NULL, NULL);
if (err)
return err;
currRead = 1;
currWrite = 1;
kernelInfo = kernelInfo->next;
}
}
return err;
} }
cl_int
clFFT_1DTwistInterleaved(clFFT_Plan Plan, cl_command_queue queue, cl_mem array,
unsigned numRows, unsigned numCols, unsigned startRow, unsigned rowsToProcess, clFFT_Direction dir)
{
cl_fft_plan *plan = (cl_fft_plan *)Plan;
unsigned int N = numRows * numCols;
unsigned int nCols = numCols;
unsigned int sRow = startRow;
unsigned int rToProcess = rowsToProcess;
int d = dir;
int err = 0;
cl_device_id device_id;
err = clGetCommandQueueInfo(queue, CL_QUEUE_DEVICE, sizeof(cl_device_id), &device_id, NULL);
if (err)
return err;
size_t gSize;
err = clGetKernelWorkGroupInfo(plan->twist_kernel, device_id, CL_KERNEL_WORK_GROUP_SIZE, sizeof(size_t), &gSize, NULL);
if (err)
return err;
gSize = min(128, gSize);
size_t numGlobalThreads[1] = {max(numCols / gSize, 1) * gSize};
size_t numLocalThreads[1] = {gSize};
err |= clSetKernelArg(plan->twist_kernel, 0, sizeof(cl_mem), &array);
err |= clSetKernelArg(plan->twist_kernel, 1, sizeof(unsigned int), &sRow);
err |= clSetKernelArg(plan->twist_kernel, 2, sizeof(unsigned int), &nCols);
err |= clSetKernelArg(plan->twist_kernel, 3, sizeof(unsigned int), &N);
err |= clSetKernelArg(plan->twist_kernel, 4, sizeof(unsigned int), &rToProcess);
err |= clSetKernelArg(plan->twist_kernel, 5, sizeof(int), &d);
err |= clEnqueueNDRangeKernel(queue, plan->twist_kernel, 1, NULL, numGlobalThreads, numLocalThreads, 0, NULL, NULL);
return err;
}
cl_int
clFFT_1DTwistPlannar(clFFT_Plan Plan, cl_command_queue queue, cl_mem array_real, cl_mem array_imag,
unsigned numRows, unsigned numCols, unsigned startRow, unsigned rowsToProcess, clFFT_Direction dir)
{
cl_fft_plan *plan = (cl_fft_plan *)Plan;
unsigned int N = numRows * numCols;
unsigned int nCols = numCols;
unsigned int sRow = startRow;
unsigned int rToProcess = rowsToProcess;
int d = dir;
int err = 0;
cl_device_id device_id;
err = clGetCommandQueueInfo(queue, CL_QUEUE_DEVICE, sizeof(cl_device_id), &device_id, NULL);
if (err)
return err;
size_t gSize;
err = clGetKernelWorkGroupInfo(plan->twist_kernel, device_id, CL_KERNEL_WORK_GROUP_SIZE, sizeof(size_t), &gSize, NULL);
if (err)
return err;
gSize = min(128, gSize);
size_t numGlobalThreads[1] = {max(numCols / gSize, 1) * gSize};
size_t numLocalThreads[1] = {gSize};
err |= clSetKernelArg(plan->twist_kernel, 0, sizeof(cl_mem), &array_real);
err |= clSetKernelArg(plan->twist_kernel, 1, sizeof(cl_mem), &array_imag);
err |= clSetKernelArg(plan->twist_kernel, 2, sizeof(unsigned int), &sRow);
err |= clSetKernelArg(plan->twist_kernel, 3, sizeof(unsigned int), &nCols);
err |= clSetKernelArg(plan->twist_kernel, 4, sizeof(unsigned int), &N);
err |= clSetKernelArg(plan->twist_kernel, 5, sizeof(unsigned int), &rToProcess);
err |= clSetKernelArg(plan->twist_kernel, 6, sizeof(int), &d);
err |= clEnqueueNDRangeKernel(queue, plan->twist_kernel, 1, NULL, numGlobalThreads, numLocalThreads, 0, NULL, NULL);
return err;
}

188
src/algorithms/libs/opencl/fft_internal.h
View File

@ -58,106 +58,106 @@ using namespace std;
typedef enum kernel_dir_t typedef enum kernel_dir_t
{ {
cl_fft_kernel_x, cl_fft_kernel_x,
cl_fft_kernel_y, cl_fft_kernel_y,
cl_fft_kernel_z cl_fft_kernel_z
}cl_fft_kernel_dir; } cl_fft_kernel_dir;
typedef struct kernel_info_t typedef struct kernel_info_t
{ {
cl_kernel kernel; cl_kernel kernel;
char *kernel_name; char *kernel_name;
unsigned lmem_size; unsigned lmem_size;
unsigned num_workgroups; unsigned num_workgroups;
unsigned num_xforms_per_workgroup; unsigned num_xforms_per_workgroup;
unsigned num_workitems_per_workgroup; unsigned num_workitems_per_workgroup;
cl_fft_kernel_dir dir; cl_fft_kernel_dir dir;
int in_place_possible; int in_place_possible;
kernel_info_t *next; kernel_info_t *next;
}cl_fft_kernel_info; } cl_fft_kernel_info;
typedef struct typedef struct
{ {
// context in which fft resources are created and kernels are executed // context in which fft resources are created and kernels are executed
cl_context context; cl_context context;
// size of signal // size of signal
clFFT_Dim3 n; clFFT_Dim3 n;
// dimension of transform ... must be either 1D, 2D or 3D // dimension of transform ... must be either 1D, 2D or 3D
clFFT_Dimension dim; clFFT_Dimension dim;
// data format ... must be either interleaved or plannar // data format ... must be either interleaved or plannar
clFFT_DataFormat format; clFFT_DataFormat format;
// string containing kernel source. Generated at runtime based on // string containing kernel source. Generated at runtime based on
// n, dim, format and other parameters // n, dim, format and other parameters
string *kernel_string; string *kernel_string;
// CL program containing source and kernel this particular // CL program containing source and kernel this particular
// n, dim, data format // n, dim, data format
cl_program program; cl_program program;
// linked list of kernels which needs to be executed for this fft // linked list of kernels which needs to be executed for this fft
cl_fft_kernel_info *kernel_info; cl_fft_kernel_info *kernel_info;
// number of kernels // number of kernels
int num_kernels; int num_kernels;
// twist kernel for virtualizing fft of very large sizes that do not // twist kernel for virtualizing fft of very large sizes that do not
// fit in GPU global memory // fit in GPU global memory
cl_kernel twist_kernel; cl_kernel twist_kernel;
// flag indicating if temporary intermediate buffer is needed or not. // flag indicating if temporary intermediate buffer is needed or not.
// this depends on fft kernels being executed and if transform is // this depends on fft kernels being executed and if transform is
// in-place or out-of-place. e.g. Local memory fft (say 1D 1024 ... // in-place or out-of-place. e.g. Local memory fft (say 1D 1024 ...
// one that does not require global transpose do not need temporary buffer) // one that does not require global transpose do not need temporary buffer)
// 2D 1024x1024 out-of-place fft however do require intermediate buffer. // 2D 1024x1024 out-of-place fft however do require intermediate buffer.
// If temp buffer is needed, its allocation is lazy i.e. its not allocated // If temp buffer is needed, its allocation is lazy i.e. its not allocated
// until its needed // until its needed
cl_int temp_buffer_needed; cl_int temp_buffer_needed;
// Batch size is runtime parameter and size of temporary buffer (if needed) // Batch size is runtime parameter and size of temporary buffer (if needed)
// depends on batch size. Allocation of temporary buffer is lazy i.e. its // depends on batch size. Allocation of temporary buffer is lazy i.e. its
// only created when needed. Once its created at first call of clFFT_Executexxx // only created when needed. Once its created at first call of clFFT_Executexxx
// it is not allocated next time if next time clFFT_Executexxx is called with // it is not allocated next time if next time clFFT_Executexxx is called with
// batch size different than the first call. last_batch_size caches the last // batch size different than the first call. last_batch_size caches the last
// batch size with which this plan is used so that we dont keep allocating/deallocating // batch size with which this plan is used so that we dont keep allocating/deallocating
// temp buffer if same batch size is used again and again. // temp buffer if same batch size is used again and again.
unsigned last_batch_size; unsigned last_batch_size;
// temporary buffer for interleaved plan // temporary buffer for interleaved plan
cl_mem tempmemobj; cl_mem tempmemobj;
// temporary buffer for planner plan. Only one of tempmemobj or // temporary buffer for planner plan. Only one of tempmemobj or
// (tempmemobj_real, tempmemobj_imag) pair is valid (allocated) depending // (tempmemobj_real, tempmemobj_imag) pair is valid (allocated) depending
// data format of plan (plannar or interleaved) // data format of plan (plannar or interleaved)
cl_mem tempmemobj_real, tempmemobj_imag; cl_mem tempmemobj_real, tempmemobj_imag;
// Maximum size of signal for which local memory transposed based // Maximum size of signal for which local memory transposed based
// fft is sufficient i.e. no global mem transpose (communication) // fft is sufficient i.e. no global mem transpose (communication)
// is needed // is needed
unsigned max_localmem_fft_size; unsigned max_localmem_fft_size;
// Maximum work items per work group allowed. This, along with max_radix below controls // Maximum work items per work group allowed. This, along with max_radix below controls
// maximum local memory being used by fft kernels of this plan. Set to 256 by default // maximum local memory being used by fft kernels of this plan. Set to 256 by default
unsigned max_work_item_per_workgroup; unsigned max_work_item_per_workgroup;
// Maximum base radix for local memory fft ... this controls the maximum register // Maximum base radix for local memory fft ... this controls the maximum register
// space used by work items. Currently defaults to 16 // space used by work items. Currently defaults to 16
unsigned max_radix; unsigned max_radix;
// Device depended parameter that tells how many work-items need to be read consecutive // Device depended parameter that tells how many work-items need to be read consecutive
// values to make sure global memory access by work-items of a work-group result in // values to make sure global memory access by work-items of a work-group result in
// coalesced memory access to utilize full bandwidth e.g. on NVidia tesla, this is 16 // coalesced memory access to utilize full bandwidth e.g. on NVidia tesla, this is 16
unsigned min_mem_coalesce_width; unsigned min_mem_coalesce_width;
// Number of local memory banks. This is used to geneate kernel with local memory // Number of local memory banks. This is used to geneate kernel with local memory
// transposes with appropriate padding to avoid bank conflicts to local memory // transposes with appropriate padding to avoid bank conflicts to local memory
// e.g. on NVidia it is 16. // e.g. on NVidia it is 16.
unsigned num_local_mem_banks; unsigned num_local_mem_banks;
}cl_fft_plan; } cl_fft_plan;
void FFT1D(cl_fft_plan *plan, cl_fft_kernel_dir dir); void FFT1D(cl_fft_plan *plan, cl_fft_kernel_dir dir);
#endif #endif

2124
src/algorithms/libs/opencl/fft_kernelstring.cc
View File

File diff suppressed because it is too large Load Diff

586
src/algorithms/libs/opencl/fft_setup.cc
View File

@ -61,59 +61,59 @@ using namespace std;
extern void getKernelWorkDimensions(cl_fft_plan *plan, cl_fft_kernel_info *kernelInfo, cl_int *batchSize, size_t *gWorkItems, size_t *lWorkItems); extern void getKernelWorkDimensions(cl_fft_plan *plan, cl_fft_kernel_info *kernelInfo, cl_int *batchSize, size_t *gWorkItems, size_t *lWorkItems);
static void static void
getBlockConfigAndKernelString(cl_fft_plan *plan) getBlockConfigAndKernelString(cl_fft_plan *plan)
{ {
plan->temp_buffer_needed = 0; plan->temp_buffer_needed = 0;
*plan->kernel_string += baseKernels; *plan->kernel_string += baseKernels;
if(plan->format == clFFT_SplitComplexFormat) if (plan->format == clFFT_SplitComplexFormat)
*plan->kernel_string += twistKernelPlannar; *plan->kernel_string += twistKernelPlannar;
else else
*plan->kernel_string += twistKernelInterleaved; *plan->kernel_string += twistKernelInterleaved;
switch(plan->dim) switch (plan->dim)
{ {
case clFFT_1D: case clFFT_1D:
FFT1D(plan, cl_fft_kernel_x); FFT1D(plan, cl_fft_kernel_x);
break; break;
case clFFT_2D: case clFFT_2D:
FFT1D(plan, cl_fft_kernel_x); FFT1D(plan, cl_fft_kernel_x);
FFT1D(plan, cl_fft_kernel_y); FFT1D(plan, cl_fft_kernel_y);
break; break;
case clFFT_3D: case clFFT_3D:
FFT1D(plan, cl_fft_kernel_x); FFT1D(plan, cl_fft_kernel_x);
FFT1D(plan, cl_fft_kernel_y); FFT1D(plan, cl_fft_kernel_y);
FFT1D(plan, cl_fft_kernel_z); FFT1D(plan, cl_fft_kernel_z);
break; break;
default: default:
return; return;
} }
plan->temp_buffer_needed = 0; plan->temp_buffer_needed = 0;
cl_fft_kernel_info *kInfo = plan->kernel_info; cl_fft_kernel_info *kInfo = plan->kernel_info;
while(kInfo) while (kInfo)
{ {
plan->temp_buffer_needed |= !kInfo->in_place_possible; plan->temp_buffer_needed |= !kInfo->in_place_possible;
kInfo = kInfo->next; kInfo = kInfo->next;
} }
} }
static void static void
deleteKernelInfo(cl_fft_kernel_info *kInfo) deleteKernelInfo(cl_fft_kernel_info *kInfo)
{ {
if(kInfo) if (kInfo)
{ {
if(kInfo->kernel_name) if (kInfo->kernel_name)
free(kInfo->kernel_name); free(kInfo->kernel_name);
if(kInfo->kernel) if (kInfo->kernel)
clReleaseKernel(kInfo->kernel); clReleaseKernel(kInfo->kernel);
free(kInfo); free(kInfo);
} }
} }
static void static void
@ -121,282 +121,282 @@ destroy_plan(cl_fft_plan *Plan)
{ {
cl_fft_kernel_info *kernel_info = Plan->kernel_info; cl_fft_kernel_info *kernel_info = Plan->kernel_info;
while(kernel_info) while (kernel_info)
{ {
cl_fft_kernel_info *tmp = kernel_info->next; cl_fft_kernel_info *tmp = kernel_info->next;
deleteKernelInfo(kernel_info); deleteKernelInfo(kernel_info);
kernel_info = tmp; kernel_info = tmp;
} }
Plan->kernel_info = NULL; Plan->kernel_info = NULL;
if(Plan->kernel_string) if (Plan->kernel_string)
{ {
delete Plan->kernel_string; delete Plan->kernel_string;
Plan->kernel_string = NULL; Plan->kernel_string = NULL;
} }
if(Plan->twist_kernel) if (Plan->twist_kernel)
{ {
clReleaseKernel(Plan->twist_kernel); clReleaseKernel(Plan->twist_kernel);
Plan->twist_kernel = NULL; Plan->twist_kernel = NULL;
} }
if(Plan->program) if (Plan->program)
{ {
clReleaseProgram(Plan->program); clReleaseProgram(Plan->program);
Plan->program = NULL; Plan->program = NULL;
} }
if(Plan->tempmemobj) if (Plan->tempmemobj)
{ {
clReleaseMemObject(Plan->tempmemobj); clReleaseMemObject(Plan->tempmemobj);
Plan->tempmemobj = NULL; Plan->tempmemobj = NULL;
} }
if(Plan->tempmemobj_real) if (Plan->tempmemobj_real)
{ {
clReleaseMemObject(Plan->tempmemobj_real); clReleaseMemObject(Plan->tempmemobj_real);
Plan->tempmemobj_real = NULL; Plan->tempmemobj_real = NULL;
} }
if(Plan->tempmemobj_imag) if (Plan->tempmemobj_imag)
{ {
clReleaseMemObject(Plan->tempmemobj_imag); clReleaseMemObject(Plan->tempmemobj_imag);
Plan->tempmemobj_imag = NULL; Plan->tempmemobj_imag = NULL;
} }
} }
static int static int
createKernelList(cl_fft_plan *plan) createKernelList(cl_fft_plan *plan)
{ {
cl_program program = plan->program; cl_program program = plan->program;
cl_fft_kernel_info *kernel_info = plan->kernel_info; cl_fft_kernel_info *kernel_info = plan->kernel_info;
cl_int err;
while(kernel_info)
{
kernel_info->kernel = clCreateKernel(program, kernel_info->kernel_name, &err);
if(!kernel_info->kernel || err != CL_SUCCESS)
return err;
kernel_info = kernel_info->next;
}
if(plan->format == clFFT_SplitComplexFormat)
plan->twist_kernel = clCreateKernel(program, "clFFT_1DTwistSplit", &err);
else
plan->twist_kernel = clCreateKernel(program, "clFFT_1DTwistInterleaved", &err);
if(!plan->twist_kernel || err)
return err;
return CL_SUCCESS; cl_int err;
while (kernel_info)
{
kernel_info->kernel = clCreateKernel(program, kernel_info->kernel_name, &err);
if (!kernel_info->kernel || err != CL_SUCCESS)
return err;
kernel_info = kernel_info->next;
}
if (plan->format == clFFT_SplitComplexFormat)
plan->twist_kernel = clCreateKernel(program, "clFFT_1DTwistSplit", &err);
else
plan->twist_kernel = clCreateKernel(program, "clFFT_1DTwistInterleaved", &err);
if (!plan->twist_kernel || err)
return err;
return CL_SUCCESS;
} }
int getMaxKernelWorkGroupSize(cl_fft_plan *plan, unsigned int *max_wg_size, unsigned int num_devices, cl_device_id *devices) int getMaxKernelWorkGroupSize(cl_fft_plan *plan, unsigned int *max_wg_size, unsigned int num_devices, cl_device_id *devices)
{ {
int reg_needed = 0; int reg_needed = 0;
*max_wg_size = std::numeric_limits<int>::max(); *max_wg_size = std::numeric_limits<int>::max();
int err; int err;
unsigned wg_size; unsigned wg_size;
unsigned int i;
for(i = 0; i < num_devices; i++)
{
cl_fft_kernel_info *kInfo = plan->kernel_info;
while(kInfo)
{
err = clGetKernelWorkGroupInfo(kInfo->kernel, devices[i], CL_KERNEL_WORK_GROUP_SIZE, sizeof(size_t), &wg_size, NULL);
if(err != CL_SUCCESS)
return -1;
if(wg_size < kInfo->num_workitems_per_workgroup)
reg_needed |= 1;
if(*max_wg_size > wg_size)
*max_wg_size = wg_size;
kInfo = kInfo->next;
}
}
return reg_needed;
}
#define ERR_MACRO(err) { \ unsigned int i;
if( err != CL_SUCCESS) \ for (i = 0; i < num_devices; i++)
{ \ {
if(error_code) \ cl_fft_kernel_info *kInfo = plan->kernel_info;
*error_code = err; \ while (kInfo)
clFFT_DestroyPlan((clFFT_Plan) plan); \ {
return (clFFT_Plan) NULL; \ err = clGetKernelWorkGroupInfo(kInfo->kernel, devices[i], CL_KERNEL_WORK_GROUP_SIZE, sizeof(size_t), &wg_size, NULL);
} \ if (err != CL_SUCCESS)
} return -1;
if (wg_size < kInfo->num_workitems_per_workgroup)
reg_needed |= 1;
if (*max_wg_size > wg_size)
*max_wg_size = wg_size;
kInfo = kInfo->next;
}
}
return reg_needed;
}
#define ERR_MACRO(err) \
{ \
if (err != CL_SUCCESS) \
{ \
if (error_code) \
*error_code = err; \
clFFT_DestroyPlan((clFFT_Plan)plan); \
return (clFFT_Plan)NULL; \
} \
}
clFFT_Plan clFFT_Plan
clFFT_CreatePlan(cl_context context, clFFT_Dim3 n, clFFT_Dimension dim, clFFT_DataFormat dataFormat, cl_int *error_code ) clFFT_CreatePlan(cl_context context, clFFT_Dim3 n, clFFT_Dimension dim, clFFT_DataFormat dataFormat, cl_int *error_code)
{ {
int i; int i;
cl_int err; cl_int err;
int isPow2 = 1; int isPow2 = 1;
cl_fft_plan *plan = NULL; cl_fft_plan *plan = NULL;
ostringstream kString; ostringstream kString;
int num_devices; int num_devices;
int gpu_found = 0; int gpu_found = 0;
cl_device_id devices[16]; cl_device_id devices[16];
size_t ret_size; size_t ret_size;
cl_device_type device_type; cl_device_type device_type;
if(!context)
ERR_MACRO(CL_INVALID_VALUE);
isPow2 |= n.x && !( (n.x - 1) & n.x );
isPow2 |= n.y && !( (n.y - 1) & n.y );
isPow2 |= n.z && !( (n.z - 1) & n.z );
if(!isPow2) if (!context)
ERR_MACRO(CL_INVALID_VALUE); ERR_MACRO(CL_INVALID_VALUE);
if( (dim == clFFT_1D && (n.y != 1 || n.z != 1)) || (dim == clFFT_2D && n.z != 1) )
ERR_MACRO(CL_INVALID_VALUE);
plan = (cl_fft_plan *) malloc(sizeof(cl_fft_plan)); isPow2 |= n.x && !((n.x - 1) & n.x);
if(!plan) isPow2 |= n.y && !((n.y - 1) & n.y);
ERR_MACRO(CL_OUT_OF_RESOURCES); isPow2 |= n.z && !((n.z - 1) & n.z);
plan->context = context;
clRetainContext(context);
plan->n = n;
plan->dim = dim;
plan->format = dataFormat;
plan->kernel_info = 0;
plan->num_kernels = 0;
plan->twist_kernel = 0;
plan->program = 0;
plan->temp_buffer_needed = 0;
plan->last_batch_size = 0;
plan->tempmemobj = 0;
plan->tempmemobj_real = 0;
plan->tempmemobj_imag = 0;
plan->max_localmem_fft_size = 2048;
plan->max_work_item_per_workgroup = 256;
plan->max_radix = 16;
plan->min_mem_coalesce_width = 16;
plan->num_local_mem_banks = 16;
patch_kernel_source:
plan->kernel_string = new string(""); if (!isPow2)
if(!plan->kernel_string) ERR_MACRO(CL_INVALID_VALUE);
if ((dim == clFFT_1D && (n.y != 1 || n.z != 1)) || (dim == clFFT_2D && n.z != 1))
ERR_MACRO(CL_INVALID_VALUE);
plan = (cl_fft_plan *)malloc(sizeof(cl_fft_plan));
if (!plan)
ERR_MACRO(CL_OUT_OF_RESOURCES); ERR_MACRO(CL_OUT_OF_RESOURCES);
getBlockConfigAndKernelString(plan); plan->context = context;
clRetainContext(context);
const char *source_str = plan->kernel_string->c_str(); plan->n = n;
plan->program = clCreateProgramWithSource(context, 1, (const char**) &source_str, NULL, &err); plan->dim = dim;
plan->format = dataFormat;
plan->kernel_info = 0;
plan->num_kernels = 0;
plan->twist_kernel = 0;
plan->program = 0;
plan->temp_buffer_needed = 0;
plan->last_batch_size = 0;
plan->tempmemobj = 0;
plan->tempmemobj_real = 0;
plan->tempmemobj_imag = 0;
plan->max_localmem_fft_size = 2048;
plan->max_work_item_per_workgroup = 256;
plan->max_radix = 16;
plan->min_mem_coalesce_width = 16;
plan->num_local_mem_banks = 16;
patch_kernel_source:
plan->kernel_string = new string("");
if (!plan->kernel_string)
ERR_MACRO(CL_OUT_OF_RESOURCES);
getBlockConfigAndKernelString(plan);
const char *source_str = plan->kernel_string->c_str();
plan->program = clCreateProgramWithSource(context, 1, (const char **)&source_str, NULL, &err);
ERR_MACRO(err); ERR_MACRO(err);
err = clGetContextInfo(context, CL_CONTEXT_DEVICES, sizeof(devices), devices, &ret_size); err = clGetContextInfo(context, CL_CONTEXT_DEVICES, sizeof(devices), devices, &ret_size);
ERR_MACRO(err);
num_devices = (int)(ret_size / sizeof(cl_device_id));
for(i = 0; i < num_devices; i++)
{
err = clGetDeviceInfo(devices[i], CL_DEVICE_TYPE, sizeof(device_type), &device_type, NULL);
ERR_MACRO(err);
if(device_type == CL_DEVICE_TYPE_GPU)
{
gpu_found = 1;
err = clBuildProgram(plan->program, 1, &devices[i], "-cl-mad-enable", NULL, NULL);
if (err != CL_SUCCESS)
{
char *build_log;
char devicename[200];
size_t log_size;
err = clGetProgramBuildInfo(plan->program, devices[i], CL_PROGRAM_BUILD_LOG, 0, NULL, &log_size);
ERR_MACRO(err);
build_log = (char *) malloc(log_size + 1);
err = clGetProgramBuildInfo(plan->program, devices[i], CL_PROGRAM_BUILD_LOG, log_size, build_log, NULL);
ERR_MACRO(err);
err = clGetDeviceInfo(devices[i], CL_DEVICE_NAME, sizeof(devicename), devicename, NULL);
ERR_MACRO(err);
fprintf(stdout, "FFT program build log on device %s\n", devicename);
fprintf(stdout, "%s\n", build_log);
free(build_log);
ERR_MACRO(err);
}
}
}
if(!gpu_found)
ERR_MACRO(CL_INVALID_CONTEXT);
err = createKernelList(plan);
ERR_MACRO(err); ERR_MACRO(err);
num_devices = (int)(ret_size / sizeof(cl_device_id));
for (i = 0; i < num_devices; i++)
{
err = clGetDeviceInfo(devices[i], CL_DEVICE_TYPE, sizeof(device_type), &device_type, NULL);
ERR_MACRO(err);
if (device_type == CL_DEVICE_TYPE_GPU)
{
gpu_found = 1;
err = clBuildProgram(plan->program, 1, &devices[i], "-cl-mad-enable", NULL, NULL);
if (err != CL_SUCCESS)
{
char *build_log;
char devicename[200];
size_t log_size;
err = clGetProgramBuildInfo(plan->program, devices[i], CL_PROGRAM_BUILD_LOG, 0, NULL, &log_size);
ERR_MACRO(err);
build_log = (char *)malloc(log_size + 1);
err = clGetProgramBuildInfo(plan->program, devices[i], CL_PROGRAM_BUILD_LOG, log_size, build_log, NULL);
ERR_MACRO(err);
err = clGetDeviceInfo(devices[i], CL_DEVICE_NAME, sizeof(devicename), devicename, NULL);
ERR_MACRO(err);
fprintf(stdout, "FFT program build log on device %s\n", devicename);
fprintf(stdout, "%s\n", build_log);
free(build_log);
ERR_MACRO(err);
}
}
}
if (!gpu_found)
ERR_MACRO(CL_INVALID_CONTEXT);
err = createKernelList(plan);
ERR_MACRO(err);
// we created program and kernels based on "some max work group size (default 256)" ... this work group size // we created program and kernels based on "some max work group size (default 256)" ... this work group size
// may be larger than what kernel may execute with ... if thats the case we need to regenerate the kernel source // may be larger than what kernel may execute with ... if thats the case we need to regenerate the kernel source
// setting this as limit i.e max group size and rebuild. // setting this as limit i.e max group size and rebuild.
unsigned int max_kernel_wg_size; unsigned int max_kernel_wg_size;
int patching_req = getMaxKernelWorkGroupSize(plan, &max_kernel_wg_size, num_devices, devices); int patching_req = getMaxKernelWorkGroupSize(plan, &max_kernel_wg_size, num_devices, devices);
if(patching_req == -1) if (patching_req == -1)
{ {
ERR_MACRO(err); ERR_MACRO(err);
} }
if(patching_req) if (patching_req)
{ {
destroy_plan(plan); destroy_plan(plan);
plan->max_work_item_per_workgroup = max_kernel_wg_size; plan->max_work_item_per_workgroup = max_kernel_wg_size;
goto patch_kernel_source; goto patch_kernel_source;
} }
cl_fft_kernel_info *kInfo = plan->kernel_info; cl_fft_kernel_info *kInfo = plan->kernel_info;
while(kInfo) while (kInfo)
{ {
plan->num_kernels++; plan->num_kernels++;
kInfo = kInfo->next; kInfo = kInfo->next;
} }
if(error_code) if (error_code)
*error_code = CL_SUCCESS; *error_code = CL_SUCCESS;
return (clFFT_Plan) plan; return (clFFT_Plan)plan;
} }
void void clFFT_DestroyPlan(clFFT_Plan plan)
clFFT_DestroyPlan(clFFT_Plan plan)
{ {
cl_fft_plan *Plan = (cl_fft_plan *) plan; cl_fft_plan *Plan = (cl_fft_plan *)plan;
if(Plan) if (Plan)
{ {
destroy_plan(Plan); destroy_plan(Plan);
clReleaseContext(Plan->context); clReleaseContext(Plan->context);
free(Plan); free(Plan);
} }
} }
void clFFT_DumpPlan( clFFT_Plan Plan, FILE *file) void clFFT_DumpPlan(clFFT_Plan Plan, FILE *file)
{ {
size_t gDim, lDim; size_t gDim, lDim;
FILE *out; FILE *out;
if(!file) if (!file)
out = stdout; out = stdout;
else else
out = file; out = file;
cl_fft_plan *plan = (cl_fft_plan *) Plan; cl_fft_plan *plan = (cl_fft_plan *)Plan;
cl_fft_kernel_info *kInfo = plan->kernel_info; cl_fft_kernel_info *kInfo = plan->kernel_info;
while(kInfo) while (kInfo)
{ {
cl_int s = 1; cl_int s = 1;
getKernelWorkDimensions(plan, kInfo, &s, &gDim, &lDim); getKernelWorkDimensions(plan, kInfo, &s, &gDim, &lDim);
fprintf(out, "Run kernel %s with global dim = {%zd*BatchSize}, local dim={%zd}\n", kInfo->kernel_name, gDim, lDim); fprintf(out, "Run kernel %s with global dim = {%zd*BatchSize}, local dim={%zd}\n", kInfo->kernel_name, gDim, lDim);
kInfo = kInfo->next; kInfo = kInfo->next;
} }
fprintf(out, "%s\n", plan->kernel_string->c_str()); fprintf(out, "%s\n", plan->kernel_string->c_str());
} }

11
src/algorithms/libs/rtklib/rtklib_rtkcmn.cc
View File

@ -253,11 +253,12 @@ const unsigned int tbl_CRC24Q[] = {
0x42FA2F, 0xC4B6D4, 0xC82F22, 0x4E63D9, 0xD11CCE, 0x575035, 0x5BC9C3, 0xDD8538}; 0x42FA2F, 0xC4B6D4, 0xC82F22, 0x4E63D9, 0xD11CCE, 0x575035, 0x5BC9C3, 0xDD8538};
extern "C" { extern "C"
void dgemm_(char *, char *, int *, int *, int *, double *, double *, int *, double *, int *, double *, double *, int *); {
extern void dgetrf_(int *, int *, double *, int *, int *, int *); void dgemm_(char *, char *, int *, int *, int *, double *, double *, int *, double *, int *, double *, double *, int *);
extern void dgetri_(int *, double *, int *, int *, double *, int *, int *); extern void dgetrf_(int *, int *, double *, int *, int *, int *);
extern void dgetrs_(char *, int *, int *, double *, int *, int *, double *, int *, int *); extern void dgetri_(int *, double *, int *, int *, double *, int *, int *);
extern void dgetrs_(char *, int *, int *, double *, int *, int *, double *, int *, int *);
} }

32
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/cmake/msvc/config.h
View File

@ -1,15 +1,15 @@
#ifndef _MSC_VER // [ #ifndef _MSC_VER // [
#error "Use this header only with Microsoft Visual C++ compilers!" #error "Use this header only with Microsoft Visual C++ compilers!"
#endif // _MSC_VER ] #endif // _MSC_VER ]
#ifndef _MSC_CONFIG_H_ // [ #ifndef _MSC_CONFIG_H_ // [
#define _MSC_CONFIG_H_ #define _MSC_CONFIG_H_
//////////////////////////////////////////////////////////////////////// ////////////////////////////////////////////////////////////////////////
// enable inline functions for C code // enable inline functions for C code
//////////////////////////////////////////////////////////////////////// ////////////////////////////////////////////////////////////////////////
#ifndef __cplusplus #ifndef __cplusplus
# define inline __inline #define inline __inline
#endif #endif
//////////////////////////////////////////////////////////////////////// ////////////////////////////////////////////////////////////////////////
@ -23,12 +23,15 @@ typedef ptrdiff_t ssize_t;
//////////////////////////////////////////////////////////////////////// ////////////////////////////////////////////////////////////////////////
#if _MSC_VER < 1800 #if _MSC_VER < 1800
#include <math.h> #include <math.h>
static inline long lrint(double x){return (long)(x > 0.0 ? x + 0.5 : x - 0.5);} static inline long lrint(double x)
static inline long lrintf(float x){return (long)(x > 0.0f ? x + 0.5f : x - 0.5f);} {
static inline long long llrint(double x){return (long long)(x > 0.0 ? x + 0.5 : x - 0.5);} return (long)(x > 0.0 ? x + 0.5 : x - 0.5);
static inline long long llrintf(float x){return (long long)(x > 0.0f ? x + 0.5f : x - 0.5f);} }
static inline double rint(double x){return (x > 0.0)? floor(x + 0.5) : ceil(x - 0.5);} static inline long lrintf(float x) { return (long)(x > 0.0f ? x + 0.5f : x - 0.5f); }
static inline float rintf(float x){return (x > 0.0f)? floorf(x + 0.5f) : ceilf(x - 0.5f);} static inline long long llrint(double x) { return (long long)(x > 0.0 ? x + 0.5 : x - 0.5); }
static inline long long llrintf(float x) { return (long long)(x > 0.0f ? x + 0.5f : x - 0.5f); }
static inline double rint(double x) { return (x > 0.0) ? floor(x + 0.5) : ceil(x - 0.5); }
static inline float rintf(float x) { return (x > 0.0f) ? floorf(x + 0.5f) : ceilf(x - 0.5f); }
#endif #endif
//////////////////////////////////////////////////////////////////////// ////////////////////////////////////////////////////////////////////////
@ -43,7 +46,10 @@ static inline float rintf(float x){return (x > 0.0f)? floorf(x + 0.5f) : ceilf(x
// random and srandom // random and srandom
//////////////////////////////////////////////////////////////////////// ////////////////////////////////////////////////////////////////////////
#include <stdlib.h> #include <stdlib.h>
static inline long int random (void) { return rand(); } static inline long int random(void)
static inline void srandom (unsigned int seed) { srand(seed); } {
return rand();
}
static inline void srandom(unsigned int seed) { srand(seed); }
#endif // _MSC_CONFIG_H_ ] #endif // _MSC_CONFIG_H_ ]

122
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr.tmpl.c
View File

@ -31,85 +31,97 @@ static intptr_t __alignment_mask = 0;
struct volk_gnsssdr_machine *get_machine(void) struct volk_gnsssdr_machine *get_machine(void)
{ {
extern struct volk_gnsssdr_machine *volk_gnsssdr_machines[]; extern struct volk_gnsssdr_machine *volk_gnsssdr_machines[];
extern unsigned int n_volk_gnsssdr_machines; extern unsigned int n_volk_gnsssdr_machines;
static struct volk_gnsssdr_machine *machine = NULL; static struct volk_gnsssdr_machine *machine = NULL;
if(machine != NULL) if (machine != NULL)
return machine; return machine;
else { else
unsigned int max_score = 0; {
unsigned int i; unsigned int max_score = 0;
struct volk_gnsssdr_machine *max_machine = NULL; unsigned int i;
for(i=0; i<n_volk_gnsssdr_machines; i++) { struct volk_gnsssdr_machine *max_machine = NULL;
if(!(volk_gnsssdr_machines[i]->caps & (~volk_gnsssdr_get_lvarch()))) { for (i = 0; i < n_volk_gnsssdr_machines; i++)
if(volk_gnsssdr_machines[i]->caps > max_score) { {
max_score = volk_gnsssdr_machines[i]->caps; if (!(volk_gnsssdr_machines[i]->caps & (~volk_gnsssdr_get_lvarch())))
max_machine = volk_gnsssdr_machines[i]; {
if (volk_gnsssdr_machines[i]->caps > max_score)
{
max_score = volk_gnsssdr_machines[i]->caps;
max_machine = volk_gnsssdr_machines[i];
}
}
}
machine = max_machine;
//printf("Using Volk machine: %s\n", machine->name);
__alignment = machine->alignment;
__alignment_mask = (intptr_t)(__alignment - 1);
return machine;
} }
}
}
machine = max_machine;
//printf("Using Volk machine: %s\n", machine->name);
__alignment = machine->alignment;
__alignment_mask = (intptr_t)(__alignment-1);
return machine;
}
} }
void volk_gnsssdr_list_machines(void) void volk_gnsssdr_list_machines(void)
{ {
extern struct volk_gnsssdr_machine *volk_gnsssdr_machines[]; extern struct volk_gnsssdr_machine *volk_gnsssdr_machines[];
extern unsigned int n_volk_gnsssdr_machines; extern unsigned int n_volk_gnsssdr_machines;
unsigned int i; unsigned int i;
for(i=0; i<n_volk_gnsssdr_machines; i++) { for (i = 0; i < n_volk_gnsssdr_machines; i++)
if(!(volk_gnsssdr_machines[i]->caps & (~volk_gnsssdr_get_lvarch()))) { {
printf("%s;", volk_gnsssdr_machines[i]->name); if (!(volk_gnsssdr_machines[i]->caps & (~volk_gnsssdr_get_lvarch())))
} {
} printf("%s;", volk_gnsssdr_machines[i]->name);
printf("\n"); }
}
printf("\n");
} }
const char* volk_gnsssdr_get_machine(void) const char *volk_gnsssdr_get_machine(void)
{ {
extern struct volk_gnsssdr_machine *volk_gnsssdr_machines[]; extern struct volk_gnsssdr_machine *volk_gnsssdr_machines[];
extern unsigned int n_volk_gnsssdr_machines; extern unsigned int n_volk_gnsssdr_machines;
static struct volk_gnsssdr_machine *machine = NULL; static struct volk_gnsssdr_machine *machine = NULL;
if(machine != NULL) if (machine != NULL)
return machine->name; return machine->name;
else { else
unsigned int max_score = 0; {
unsigned int i; unsigned int max_score = 0;
struct volk_gnsssdr_machine *max_machine = NULL; unsigned int i;
for(i=0; i<n_volk_gnsssdr_machines; i++) { struct volk_gnsssdr_machine *max_machine = NULL;
if(!(volk_gnsssdr_machines[i]->caps & (~volk_gnsssdr_get_lvarch()))) { for (i = 0; i < n_volk_gnsssdr_machines; i++)
if(volk_gnsssdr_machines[i]->caps > max_score) { {
max_score = volk_gnsssdr_machines[i]->caps; if (!(volk_gnsssdr_machines[i]->caps & (~volk_gnsssdr_get_lvarch())))
max_machine = volk_gnsssdr_machines[i]; {
if (volk_gnsssdr_machines[i]->caps > max_score)
{
max_score = volk_gnsssdr_machines[i]->caps;
max_machine = volk_gnsssdr_machines[i];
}
}
}
machine = max_machine;
return machine->name;
} }
}
}
machine = max_machine;
return machine->name;
}
} }
size_t volk_gnsssdr_get_alignment(void) size_t volk_gnsssdr_get_alignment(void)
{ {
get_machine(); //ensures alignment is set get_machine(); //ensures alignment is set
return __alignment; return __alignment;
} }
bool volk_gnsssdr_is_aligned(const void *ptr) bool volk_gnsssdr_is_aligned(const void *ptr)
{ {
return ((intptr_t)(ptr) & __alignment_mask) == 0; return ((intptr_t)(ptr)&__alignment_mask) == 0;
} }
#define LV_HAVE_GENERIC #define LV_HAVE_GENERIC
#define LV_HAVE_DISPATCHER #define LV_HAVE_DISPATCHER
// clang-format off
%for kern in kernels: %for kern in kernels:
%if kern.has_dispatcher: %if kern.has_dispatcher:
@ -190,6 +202,8 @@ void ${kern.name}_manual(${kern.arglist_full}, const char* impl_name)
); );
} }
volk_gnsssdr_func_desc_t ${kern.name}_get_func_desc(void) { volk_gnsssdr_func_desc_t ${kern.name}_get_func_desc(void) {
const char **impl_names = get_machine()->${kern.name}_impl_names; const char **impl_names = get_machine()->${kern.name}_impl_names;
const int *impl_deps = get_machine()->${kern.name}_impl_deps; const int *impl_deps = get_machine()->${kern.name}_impl_deps;
@ -205,3 +219,5 @@ volk_gnsssdr_func_desc_t ${kern.name}_get_func_desc(void) {
} }
%endfor %endfor
// clang-format on

4
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr.tmpl.h
View File

@ -42,7 +42,7 @@ typedef struct volk_gnsssdr_func_desc
VOLK_API void volk_gnsssdr_list_machines(void); VOLK_API void volk_gnsssdr_list_machines(void);
//! Returns the name of the machine this instance will use //! Returns the name of the machine this instance will use
VOLK_API const char* volk_gnsssdr_get_machine(void); VOLK_API const char *volk_gnsssdr_get_machine(void);
//! Get the machine alignment in bytes //! Get the machine alignment in bytes
VOLK_API size_t volk_gnsssdr_get_alignment(void); VOLK_API size_t volk_gnsssdr_get_alignment(void);
@ -73,6 +73,7 @@ VOLK_API bool volk_gnsssdr_is_aligned(const void *ptr);
//! A function pointer to the dispatcher implementation //! A function pointer to the dispatcher implementation
extern VOLK_API ${kern.pname} ${kern.name}; extern VOLK_API ${kern.pname} ${kern.name};
// clang-format off
//! A function pointer to the fastest aligned implementation //! A function pointer to the fastest aligned implementation
extern VOLK_API ${kern.pname} ${kern.name}_a; extern VOLK_API ${kern.pname} ${kern.name}_a;
@ -85,6 +86,7 @@ extern VOLK_API void ${kern.name}_manual(${kern.arglist_full}, const char* impl_
//! Get description parameters for this kernel //! Get description parameters for this kernel
extern VOLK_API volk_gnsssdr_func_desc_t ${kern.name}_get_func_desc(void); extern VOLK_API volk_gnsssdr_func_desc_t ${kern.name}_get_func_desc(void);
%endfor %endfor
// clang-format off
__VOLK_DECL_END __VOLK_DECL_END

3
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_config_fixed.tmpl.h
View File

@ -19,10 +19,11 @@
#ifndef INCLUDED_VOLK_GNSSSDR_CONFIG_FIXED_H #ifndef INCLUDED_VOLK_GNSSSDR_CONFIG_FIXED_H
#define INCLUDED_VOLK_GNSSSDR_CONFIG_FIXED_H #define INCLUDED_VOLK_GNSSSDR_CONFIG_FIXED_H
// clang-format off
%for i, arch in enumerate(archs): %for i, arch in enumerate(archs):
//#ifndef LV_${arch.name.upper()} //#ifndef LV_${arch.name.upper()}
#define LV_${arch.name.upper()} ${i} #define LV_${arch.name.upper()} ${i}
//#endif //#endif
%endfor %endfor
// clang-format on
#endif /*INCLUDED_VOLK_GNSSSDR_CONFIG_FIXED*/ #endif /*INCLUDED_VOLK_GNSSSDR_CONFIG_FIXED*/

98
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_cpu.tmpl.c
View File

@ -24,50 +24,54 @@
struct VOLK_CPU volk_gnsssdr_cpu; struct VOLK_CPU volk_gnsssdr_cpu;
#if defined(__i386__) || defined(__x86_64__) || defined(_M_IX86) || defined(_M_X64) #if defined(__i386__) || defined(__x86_64__) || defined(_M_IX86) || defined(_M_X64)
#define VOLK_CPU_x86 #define VOLK_CPU_x86
#endif #endif
#if defined(VOLK_CPU_x86) #if defined(VOLK_CPU_x86)
//implement get cpuid for gcc compilers using a system or local copy of cpuid.h //implement get cpuid for gcc compilers using a system or local copy of cpuid.h
#if defined(__GNUC__) #if defined(__GNUC__)
#include <cpuid.h> #include <cpuid.h>
#define cpuid_x86(op, r) __get_cpuid(op, (unsigned int *)r+0, (unsigned int *)r+1, (unsigned int *)r+2, (unsigned int *)r+3) #define cpuid_x86(op, r) __get_cpuid(op, (unsigned int *)r + 0, (unsigned int *)r + 1, (unsigned int *)r + 2, (unsigned int *)r + 3)
#define cpuid_x86_count(op, count, regs) __cpuid_count(op, count, *((unsigned int*)regs), *((unsigned int*)regs+1), *((unsigned int*)regs+2), *((unsigned int*)regs+3)) #define cpuid_x86_count(op, count, regs) __cpuid_count(op, count, *((unsigned int *)regs), *((unsigned int *)regs + 1), *((unsigned int *)regs + 2), *((unsigned int *)regs + 3))
/* Return Intel AVX extended CPU capabilities register. /* Return Intel AVX extended CPU capabilities register.
* This function will bomb on non-AVX-capable machines, so * This function will bomb on non-AVX-capable machines, so
* check for AVX capability before executing. * check for AVX capability before executing.
*/ */
#if ((__GNUC__ > 4 || __GNUC__ == 4 && __GNUC_MINOR__ >= 2) || (__clang_major__ >= 3)) && defined(HAVE_XGETBV) #if ((__GNUC__ > 4 || __GNUC__ == 4 && __GNUC_MINOR__ >= 2) || (__clang_major__ >= 3)) && defined(HAVE_XGETBV)
static inline unsigned long long _xgetbv(unsigned int index){ static inline unsigned long long _xgetbv(unsigned int index)
unsigned int eax, edx; {
__VOLK_ASM __VOLK_VOLATILE ("xgetbv" : "=a"(eax), "=d"(edx) : "c"(index)); unsigned int eax, edx;
return ((unsigned long long)edx << 32) | eax; __VOLK_ASM __VOLK_VOLATILE("xgetbv"
} : "=a"(eax), "=d"(edx)
#define __xgetbv() _xgetbv(0) : "c"(index));
#else return ((unsigned long long)edx << 32) | eax;
#define __xgetbv() 0 }
#endif #define __xgetbv() _xgetbv(0)
#else
#define __xgetbv() 0
#endif
//implement get cpuid for MSVC compilers using __cpuid intrinsic //implement get cpuid for MSVC compilers using __cpuid intrinsic
#elif defined(_MSC_VER) && defined(HAVE_INTRIN_H) #elif defined(_MSC_VER) && defined(HAVE_INTRIN_H)
#include <intrin.h> #include <intrin.h>
#define cpuid_x86(op, r) __cpuid(((int*)r), op) #define cpuid_x86(op, r) __cpuid(((int *)r), op)
#if defined(_XCR_XFEATURE_ENABLED_MASK) #if defined(_XCR_XFEATURE_ENABLED_MASK)
#define __xgetbv() _xgetbv(_XCR_XFEATURE_ENABLED_MASK) #define __xgetbv() _xgetbv(_XCR_XFEATURE_ENABLED_MASK)
#else #else
#define __xgetbv() 0 #define __xgetbv() 0
#endif #endif
#else #else
#error "A get cpuid for volk_gnsssdr is not available on this compiler..." #error "A get cpuid for volk_gnsssdr is not available on this compiler..."
#endif //defined(__GNUC__) #endif //defined(__GNUC__)
#endif //defined(VOLK_CPU_x86) #endif //defined(VOLK_CPU_x86)
static inline unsigned int cpuid_count_x86_bit(unsigned int level, unsigned int count, unsigned int reg, unsigned int bit) { static inline unsigned int cpuid_count_x86_bit(unsigned int level, unsigned int count, unsigned int reg, unsigned int bit)
{
#if defined(VOLK_CPU_x86) #if defined(VOLK_CPU_x86)
unsigned int regs[4] = {0}; unsigned int regs[4] = {0};
cpuid_x86_count(level, count, regs); cpuid_x86_count(level, count, regs);
@ -77,10 +81,11 @@ static inline unsigned int cpuid_count_x86_bit(unsigned int level, unsigned int
#endif #endif
} }
static inline unsigned int cpuid_x86_bit(unsigned int reg, unsigned int op, unsigned int bit) { static inline unsigned int cpuid_x86_bit(unsigned int reg, unsigned int op, unsigned int bit)
{
#if defined(VOLK_CPU_x86) #if defined(VOLK_CPU_x86)
unsigned int regs[4]; unsigned int regs[4];
memset(regs, 0, sizeof(unsigned int)*4); memset(regs, 0, sizeof(unsigned int) * 4);
cpuid_x86(op, regs); cpuid_x86(op, regs);
return regs[reg] >> bit & 0x01; return regs[reg] >> bit & 0x01;
#else #else
@ -88,10 +93,11 @@ static inline unsigned int cpuid_x86_bit(unsigned int reg, unsigned int op, unsi
#endif #endif
} }
static inline unsigned int check_extended_cpuid(unsigned int val) { static inline unsigned int check_extended_cpuid(unsigned int val)
{
#if defined(VOLK_CPU_x86) #if defined(VOLK_CPU_x86)
unsigned int regs[4]; unsigned int regs[4];
memset(regs, 0, sizeof(unsigned int)*4); memset(regs, 0, sizeof(unsigned int) * 4);
cpuid_x86(0x80000000, regs); cpuid_x86(0x80000000, regs);
return regs[0] >= val; return regs[0] >= val;
#else #else
@ -99,7 +105,8 @@ static inline unsigned int check_extended_cpuid(unsigned int val) {
#endif #endif
} }
static inline unsigned int get_avx_enabled(void) { static inline unsigned int get_avx_enabled(void)
{
#if defined(VOLK_CPU_x86) #if defined(VOLK_CPU_x86)
return __xgetbv() & 0x6; return __xgetbv() & 0x6;
#else #else
@ -107,7 +114,8 @@ static inline unsigned int get_avx_enabled(void) {
#endif #endif
} }
static inline unsigned int get_avx2_enabled(void) { static inline unsigned int get_avx2_enabled(void)
{
#if defined(VOLK_CPU_x86) #if defined(VOLK_CPU_x86)
return __xgetbv() & 0x6; return __xgetbv() & 0x6;
#else #else
@ -117,28 +125,30 @@ static inline unsigned int get_avx2_enabled(void) {
//neon detection is linux specific //neon detection is linux specific
#if defined(__arm__) && defined(__linux__) #if defined(__arm__) && defined(__linux__)
#include <asm/hwcap.h> #include <asm/hwcap.h>
#include <linux/auxvec.h> #include <linux/auxvec.h>
#include <stdio.h> #include <stdio.h>
#define VOLK_CPU_ARM #define VOLK_CPU_ARM
#endif #endif
static int has_neon(void){ static int has_neon(void)
{
#if defined(VOLK_CPU_ARM) #if defined(VOLK_CPU_ARM)
FILE *auxvec_f; FILE *auxvec_f;
unsigned long auxvec[2]; unsigned long auxvec[2];
unsigned int found_neon = 0; unsigned int found_neon = 0;
auxvec_f = fopen("/proc/self/auxv", "rb"); auxvec_f = fopen("/proc/self/auxv", "rb");
if(!auxvec_f) return 0; if (!auxvec_f) return 0;
size_t r = 1; size_t r = 1;
//so auxv is basically 32b of ID and 32b of value //so auxv is basically 32b of ID and 32b of value
//so it goes like this //so it goes like this
while(!found_neon && r) { while (!found_neon && r)
r = fread(auxvec, sizeof(unsigned long), 2, auxvec_f); {
if((auxvec[0] == AT_HWCAP) && (auxvec[1] & HWCAP_NEON)) r = fread(auxvec, sizeof(unsigned long), 2, auxvec_f);
found_neon = 1; if ((auxvec[0] == AT_HWCAP) && (auxvec[1] & HWCAP_NEON))
} found_neon = 1;
}
fclose(auxvec_f); fclose(auxvec_f);
return found_neon; return found_neon;
@ -146,6 +156,7 @@ static int has_neon(void){
return 0; return 0;
#endif #endif
} }
// clang-format off
%for arch in archs: %for arch in archs:
static int i_can_has_${arch.name} (void) { static int i_can_has_${arch.name} (void) {
@ -195,3 +206,4 @@ unsigned int volk_gnsssdr_get_lvarch() {
%endfor %endfor
return retval; return retval;
} }
// clang-format on

6
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_cpu.tmpl.h
View File

@ -23,16 +23,18 @@
__VOLK_DECL_BEGIN __VOLK_DECL_BEGIN
// clang-format off
struct VOLK_CPU { struct VOLK_CPU {
%for arch in archs: %for arch in archs:
int (*has_${arch.name}) (); int (*has_${arch.name}) ();
%endfor %endfor
}; };
// clang-format on
extern struct VOLK_CPU volk_gnsssdr_cpu; extern struct VOLK_CPU volk_gnsssdr_cpu;
void volk_gnsssdr_cpu_init (); void volk_gnsssdr_cpu_init();
unsigned int volk_gnsssdr_get_lvarch (); unsigned int volk_gnsssdr_get_lvarch();
__VOLK_DECL_END __VOLK_DECL_END

4
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_machine_xxx.tmpl.c
View File

@ -16,6 +16,8 @@
* along with GNSS-SDR. If not, see <http://www.gnu.org/licenses/>. * along with GNSS-SDR. If not, see <http://www.gnu.org/licenses/>.
*/ */
// clang-format off
<% this_machine = machine_dict[args[0]] %> <% this_machine = machine_dict[args[0]] %>
<% arch_names = this_machine.arch_names %> <% arch_names = this_machine.arch_names %>
@ -31,6 +33,7 @@
#include "config.h" #include "config.h"
#endif #endif
%for kern in kernels: %for kern in kernels:
#include <volk_gnsssdr/${kern.name}.h> #include <volk_gnsssdr/${kern.name}.h>
%endfor %endfor
@ -56,3 +59,4 @@ struct volk_gnsssdr_machine volk_gnsssdr_machine_${this_machine.name} = {
<% len_impls = len(impls) %> ${len_impls}, <% len_impls = len(impls) %> ${len_impls},
%endfor %endfor
}; };
// clang-format on

5
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_machines.tmpl.c
View File

@ -20,6 +20,7 @@
#include <volk_gnsssdr/volk_gnsssdr_typedefs.h> #include <volk_gnsssdr/volk_gnsssdr_typedefs.h>
#include "volk_gnsssdr_machines.h" #include "volk_gnsssdr_machines.h"
// clang-format off
struct volk_gnsssdr_machine *volk_gnsssdr_machines[] = { struct volk_gnsssdr_machine *volk_gnsssdr_machines[] = {
%for machine in machines: %for machine in machines:
#ifdef LV_MACHINE_${machine.name.upper()} #ifdef LV_MACHINE_${machine.name.upper()}
@ -27,5 +28,5 @@ struct volk_gnsssdr_machine *volk_gnsssdr_machines[] = {
#endif #endif
%endfor %endfor
}; };
// clang-format on
unsigned int n_volk_gnsssdr_machines = sizeof(volk_gnsssdr_machines)/sizeof(*volk_gnsssdr_machines); unsigned int n_volk_gnsssdr_machines = sizeof(volk_gnsssdr_machines) / sizeof(*volk_gnsssdr_machines);

4
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_machines.tmpl.h
View File

@ -27,6 +27,7 @@
__VOLK_DECL_BEGIN __VOLK_DECL_BEGIN
// clang-format off
struct volk_gnsssdr_machine { struct volk_gnsssdr_machine {
const unsigned int caps; //capabilities (i.e., archs compiled into this machine, in the volk_gnsssdr_get_lvarch format) const unsigned int caps; //capabilities (i.e., archs compiled into this machine, in the volk_gnsssdr_get_lvarch format)
const char *name; const char *name;
@ -48,5 +49,6 @@ extern struct volk_gnsssdr_machine volk_gnsssdr_machine_${machine.name};
%endfor %endfor
__VOLK_DECL_END __VOLK_DECL_END
// clang-format on
#endif //INCLUDED_LIBVOLK_GNSSSDR_MACHINES_H #endif //INCLUDED_LIBVOLK_GNSSSDR_MACHINES_H

2
src/algorithms/libs/volk_gnsssdr_module/volk_gnsssdr/tmpl/volk_gnsssdr_typedefs.tmpl.h
View File

@ -22,8 +22,10 @@
#include <inttypes.h> #include <inttypes.h>
#include <volk_gnsssdr/volk_gnsssdr_complex.h> #include <volk_gnsssdr/volk_gnsssdr_complex.h>
// clang-format off
%for kern in kernels: %for kern in kernels:
typedef void (*${kern.pname})(${kern.arglist_types}); typedef void (*${kern.pname})(${kern.arglist_types});
%endfor %endfor
// clang-format on
#endif /*INCLUDED_VOLK_GNSSSDR_TYPEDEFS*/ #endif /*INCLUDED_VOLK_GNSSSDR_TYPEDEFS*/

3
src/algorithms/telemetry_decoder/gnuradio_blocks/gps_l2c_telemetry_decoder_cc.h
View File

@ -45,7 +45,8 @@
#include <vector> #include <vector>
extern "C" { extern "C"
{
#include "cnav_msg.h" #include "cnav_msg.h"
#include "edc.h" #include "edc.h"
#include "bits.h" #include "bits.h"

3
src/algorithms/telemetry_decoder/gnuradio_blocks/gps_l5_telemetry_decoder_cc.h
View File

@ -42,7 +42,8 @@
#include <utility> #include <utility>
#include <vector> #include <vector>
extern "C" { extern "C"
{
#include "cnav_msg.h" #include "cnav_msg.h"
#include "edc.h" #include "edc.h"
#include "bits.h" #include "bits.h"

6
src/algorithms/tracking/libs/cuda_multicorrelator.h
View File

@ -76,9 +76,9 @@ struct GPU_Complex
} }
CUDA_CALLABLE_MEMBER_DEVICE void multiply_acc(const GPU_Complex& a, const GPU_Complex& b) CUDA_CALLABLE_MEMBER_DEVICE void multiply_acc(const GPU_Complex& a, const GPU_Complex& b)
{ {
//c=a*b+c //c=a*b+c
//real part //real part
//c.r=(a.r*b.r - a.i*b.i)+c.r //c.r=(a.r*b.r - a.i*b.i)+c.r
#ifdef __CUDACC__ #ifdef __CUDACC__
r = __fmaf_rn(a.r, b.r, r); r = __fmaf_rn(a.r, b.r, r);
r = __fmaf_rn(-a.i, b.i, r); r = __fmaf_rn(-a.i, b.i, r);

3
src/core/libs/gnss_sdr_supl_client.h
View File

@ -34,7 +34,8 @@
#ifndef GNSS_SDR_SUPL_CLIENT_H_ #ifndef GNSS_SDR_SUPL_CLIENT_H_
#define GNSS_SDR_SUPL_CLIENT_H_ #define GNSS_SDR_SUPL_CLIENT_H_
extern "C" { extern "C"
{
#include "supl.h" #include "supl.h"
} }
#include "GPS_L1_CA.h" #include "GPS_L1_CA.h"

29
src/core/libs/supl/asn-rrlp/Accuracy.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Accuracy */ /* Accuracy */
typedef long Accuracy_t; typedef long Accuracy_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_Accuracy; extern asn_TYPE_descriptor_t asn_DEF_Accuracy;
asn_struct_free_f Accuracy_free; asn_struct_free_f Accuracy_free;
asn_struct_print_f Accuracy_print; asn_struct_print_f Accuracy_print;
asn_constr_check_f Accuracy_constraint; asn_constr_check_f Accuracy_constraint;
ber_type_decoder_f Accuracy_decode_ber; ber_type_decoder_f Accuracy_decode_ber;
der_type_encoder_f Accuracy_encode_der; der_type_encoder_f Accuracy_encode_der;
xer_type_decoder_f Accuracy_decode_xer; xer_type_decoder_f Accuracy_decode_xer;
xer_type_encoder_f Accuracy_encode_xer; xer_type_encoder_f Accuracy_encode_xer;
per_type_decoder_f Accuracy_decode_uper; per_type_decoder_f Accuracy_decode_uper;
per_type_encoder_f Accuracy_encode_uper; per_type_encoder_f Accuracy_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

21
src/core/libs/supl/asn-rrlp/AccuracyOpt.h
View File

@ -15,20 +15,21 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AccuracyOpt */ /* AccuracyOpt */
typedef struct AccuracyOpt typedef struct AccuracyOpt
{ {
Accuracy_t *accuracy /* OPTIONAL */; Accuracy_t *accuracy /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AccuracyOpt_t; } AccuracyOpt_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AccuracyOpt; extern asn_TYPE_descriptor_t asn_DEF_AccuracyOpt;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/AcquisAssist.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AcquisAssist */ /* AcquisAssist */
typedef struct AcquisAssist typedef struct AcquisAssist
{ {
TimeRelation_t timeRelation; TimeRelation_t timeRelation;
SeqOfAcquisElement_t acquisList; SeqOfAcquisElement_t acquisList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AcquisAssist_t; } AcquisAssist_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AcquisAssist; extern asn_TYPE_descriptor_t asn_DEF_AcquisAssist;
#ifdef __cplusplus #ifdef __cplusplus
} }

41
src/core/libs/supl/asn-rrlp/AcquisElement.h
View File

@ -16,31 +16,32 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct AddionalDopplerFields; struct AddionalDopplerFields;
struct AddionalAngleFields; struct AddionalAngleFields;
/* AcquisElement */ /* AcquisElement */
typedef struct AcquisElement typedef struct AcquisElement
{ {
SatelliteID_t svid; SatelliteID_t svid;
long doppler0; long doppler0;
struct AddionalDopplerFields *addionalDoppler /* OPTIONAL */; struct AddionalDopplerFields *addionalDoppler /* OPTIONAL */;
long codePhase; long codePhase;
long intCodePhase; long intCodePhase;
long gpsBitNumber; long gpsBitNumber;
long codePhaseSearchWindow; long codePhaseSearchWindow;
struct AddionalAngleFields *addionalAngle /* OPTIONAL */; struct AddionalAngleFields *addionalAngle /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AcquisElement_t; } AcquisElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AcquisElement; extern asn_TYPE_descriptor_t asn_DEF_AcquisElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/AddionalAngleFields.h
View File

@ -15,21 +15,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AddionalAngleFields */ /* AddionalAngleFields */
typedef struct AddionalAngleFields typedef struct AddionalAngleFields
{ {
long azimuth; long azimuth;
long elevation; long elevation;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AddionalAngleFields_t; } AddionalAngleFields_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AddionalAngleFields; extern asn_TYPE_descriptor_t asn_DEF_AddionalAngleFields;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/AddionalDopplerFields.h
View File

@ -15,21 +15,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AddionalDopplerFields */ /* AddionalDopplerFields */
typedef struct AddionalDopplerFields typedef struct AddionalDopplerFields
{ {
long doppler1; long doppler1;
long dopplerUncertainty; long dopplerUncertainty;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AddionalDopplerFields_t; } AddionalDopplerFields_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AddionalDopplerFields; extern asn_TYPE_descriptor_t asn_DEF_AddionalDopplerFields;
#ifdef __cplusplus #ifdef __cplusplus
} }

27
src/core/libs/supl/asn-rrlp/AdditionalAssistanceData.h
View File

@ -17,26 +17,27 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AdditionalAssistanceData */ /* AdditionalAssistanceData */
typedef struct AdditionalAssistanceData typedef struct AdditionalAssistanceData
{ {
GPSAssistanceData_t *gpsAssistanceData /* OPTIONAL */; GPSAssistanceData_t *gpsAssistanceData /* OPTIONAL */;
ExtensionContainer_t *extensionContainer /* OPTIONAL */; ExtensionContainer_t *extensionContainer /* OPTIONAL */;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
GANSSAssistanceData_t *ganssAssistanceData /* OPTIONAL */; GANSSAssistanceData_t *ganssAssistanceData /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AdditionalAssistanceData_t; } AdditionalAssistanceData_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AdditionalAssistanceData; extern asn_TYPE_descriptor_t asn_DEF_AdditionalAssistanceData;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/AdditionalDopplerFields.h
View File

@ -15,21 +15,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AdditionalDopplerFields */ /* AdditionalDopplerFields */
typedef struct AdditionalDopplerFields typedef struct AdditionalDopplerFields
{ {
long doppler1; long doppler1;
long dopplerUncertainty; long dopplerUncertainty;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AdditionalDopplerFields_t; } AdditionalDopplerFields_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AdditionalDopplerFields; extern asn_TYPE_descriptor_t asn_DEF_AdditionalDopplerFields;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/AlertFlag.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AlertFlag */ /* AlertFlag */
typedef long AlertFlag_t; typedef long AlertFlag_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AlertFlag; extern asn_TYPE_descriptor_t asn_DEF_AlertFlag;
asn_struct_free_f AlertFlag_free; asn_struct_free_f AlertFlag_free;
asn_struct_print_f AlertFlag_print; asn_struct_print_f AlertFlag_print;
asn_constr_check_f AlertFlag_constraint; asn_constr_check_f AlertFlag_constraint;
ber_type_decoder_f AlertFlag_decode_ber; ber_type_decoder_f AlertFlag_decode_ber;
der_type_encoder_f AlertFlag_encode_der; der_type_encoder_f AlertFlag_encode_der;
xer_type_decoder_f AlertFlag_decode_xer; xer_type_decoder_f AlertFlag_decode_xer;
xer_type_encoder_f AlertFlag_encode_xer; xer_type_encoder_f AlertFlag_encode_xer;
per_type_decoder_f AlertFlag_decode_uper; per_type_decoder_f AlertFlag_decode_uper;
per_type_encoder_f AlertFlag_encode_uper; per_type_encoder_f AlertFlag_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

39
src/core/libs/supl/asn-rrlp/Almanac-KeplerianSet.h
View File

@ -15,29 +15,30 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Almanac-KeplerianSet */ /* Almanac-KeplerianSet */
typedef struct Almanac_KeplerianSet typedef struct Almanac_KeplerianSet
{ {
long kepAlmanacE; long kepAlmanacE;
long kepAlmanacDeltaI; long kepAlmanacDeltaI;
long kepAlmanacOmegaDot; long kepAlmanacOmegaDot;
long kepSVHealth; long kepSVHealth;
long kepAlmanacAPowerHalf; long kepAlmanacAPowerHalf;
long kepAlmanacOmega0; long kepAlmanacOmega0;
long kepAlmanacW; long kepAlmanacW;
long kepAlmanacM0; long kepAlmanacM0;
long kepAlmanacAF0; long kepAlmanacAF0;
long kepAlmanacAF1; long kepAlmanacAF1;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} Almanac_KeplerianSet_t; } Almanac_KeplerianSet_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_Almanac_KeplerianSet; extern asn_TYPE_descriptor_t asn_DEF_Almanac_KeplerianSet;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/Almanac.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Almanac */ /* Almanac */
typedef struct Almanac typedef struct Almanac
{ {
long alamanacWNa; long alamanacWNa;
SeqOfAlmanacElement_t almanacList; SeqOfAlmanacElement_t almanacList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} Almanac_t; } Almanac_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_Almanac; extern asn_TYPE_descriptor_t asn_DEF_Almanac;
#ifdef __cplusplus #ifdef __cplusplus
} }

43
src/core/libs/supl/asn-rrlp/AlmanacElement.h
View File

@ -16,31 +16,32 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AlmanacElement */ /* AlmanacElement */
typedef struct AlmanacElement typedef struct AlmanacElement
{ {
SatelliteID_t satelliteID; SatelliteID_t satelliteID;
long almanacE; long almanacE;
long alamanacToa; long alamanacToa;
long almanacKsii; long almanacKsii;
long almanacOmegaDot; long almanacOmegaDot;
long almanacSVhealth; long almanacSVhealth;
long almanacAPowerHalf; long almanacAPowerHalf;
long almanacOmega0; long almanacOmega0;
long almanacW; long almanacW;
long almanacM0; long almanacM0;
long almanacAF0; long almanacAF0;
long almanacAF1; long almanacAF1;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AlmanacElement_t; } AlmanacElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AlmanacElement; extern asn_TYPE_descriptor_t asn_DEF_AlmanacElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/AntiSpoofFlag.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AntiSpoofFlag */ /* AntiSpoofFlag */
typedef long AntiSpoofFlag_t; typedef long AntiSpoofFlag_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AntiSpoofFlag; extern asn_TYPE_descriptor_t asn_DEF_AntiSpoofFlag;
asn_struct_free_f AntiSpoofFlag_free; asn_struct_free_f AntiSpoofFlag_free;
asn_struct_print_f AntiSpoofFlag_print; asn_struct_print_f AntiSpoofFlag_print;
asn_constr_check_f AntiSpoofFlag_constraint; asn_constr_check_f AntiSpoofFlag_constraint;
ber_type_decoder_f AntiSpoofFlag_decode_ber; ber_type_decoder_f AntiSpoofFlag_decode_ber;
der_type_encoder_f AntiSpoofFlag_encode_der; der_type_encoder_f AntiSpoofFlag_encode_der;
xer_type_decoder_f AntiSpoofFlag_decode_xer; xer_type_decoder_f AntiSpoofFlag_decode_xer;
xer_type_encoder_f AntiSpoofFlag_encode_xer; xer_type_encoder_f AntiSpoofFlag_encode_xer;
per_type_decoder_f AntiSpoofFlag_decode_uper; per_type_decoder_f AntiSpoofFlag_decode_uper;
per_type_encoder_f AntiSpoofFlag_encode_uper; per_type_encoder_f AntiSpoofFlag_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/AssistBTSData-R98-ExpOTD.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* AssistBTSData-R98-ExpOTD */ /* AssistBTSData-R98-ExpOTD */
typedef struct AssistBTSData_R98_ExpOTD typedef struct AssistBTSData_R98_ExpOTD
{ {
ExpectedOTD_t expectedOTD; ExpectedOTD_t expectedOTD;
ExpOTDUncertainty_t expOTDuncertainty; ExpOTDUncertainty_t expOTDuncertainty;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AssistBTSData_R98_ExpOTD_t; } AssistBTSData_R98_ExpOTD_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AssistBTSData_R98_ExpOTD; extern asn_TYPE_descriptor_t asn_DEF_AssistBTSData_R98_ExpOTD;
#ifdef __cplusplus #ifdef __cplusplus
} }

33
src/core/libs/supl/asn-rrlp/AssistBTSData.h
View File

@ -18,27 +18,28 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct CalcAssistanceBTS; struct CalcAssistanceBTS;
/* AssistBTSData */ /* AssistBTSData */
typedef struct AssistBTSData typedef struct AssistBTSData
{ {
BSIC_t bsic; BSIC_t bsic;
MultiFrameOffset_t multiFrameOffset; MultiFrameOffset_t multiFrameOffset;
TimeSlotScheme_t timeSlotScheme; TimeSlotScheme_t timeSlotScheme;
RoughRTD_t roughRTD; RoughRTD_t roughRTD;
struct CalcAssistanceBTS *calcAssistanceBTS /* OPTIONAL */; struct CalcAssistanceBTS *calcAssistanceBTS /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AssistBTSData_t; } AssistBTSData_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AssistBTSData; extern asn_TYPE_descriptor_t asn_DEF_AssistBTSData;
#ifdef __cplusplus #ifdef __cplusplus
} }

51
src/core/libs/supl/asn-rrlp/AssistanceData.h
View File

@ -16,39 +16,40 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct ReferenceAssistData; struct ReferenceAssistData;
struct MsrAssistData; struct MsrAssistData;
struct SystemInfoAssistData; struct SystemInfoAssistData;
struct GPS_AssistData; struct GPS_AssistData;
struct Rel98_AssistanceData_Extension; struct Rel98_AssistanceData_Extension;
struct Rel5_AssistanceData_Extension; struct Rel5_AssistanceData_Extension;
/* AssistanceData */ /* AssistanceData */
typedef struct AssistanceData typedef struct AssistanceData
{ {
struct ReferenceAssistData *referenceAssistData /* OPTIONAL */; struct ReferenceAssistData *referenceAssistData /* OPTIONAL */;
struct MsrAssistData *msrAssistData /* OPTIONAL */; struct MsrAssistData *msrAssistData /* OPTIONAL */;
struct SystemInfoAssistData *systemInfoAssistData /* OPTIONAL */; struct SystemInfoAssistData *systemInfoAssistData /* OPTIONAL */;
struct GPS_AssistData *gps_AssistData /* OPTIONAL */; struct GPS_AssistData *gps_AssistData /* OPTIONAL */;
MoreAssDataToBeSent_t *moreAssDataToBeSent /* OPTIONAL */; MoreAssDataToBeSent_t *moreAssDataToBeSent /* OPTIONAL */;
ExtensionContainer_t *extensionContainer /* OPTIONAL */; ExtensionContainer_t *extensionContainer /* OPTIONAL */;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
struct Rel98_AssistanceData_Extension *rel98_AssistanceData_Extension /* OPTIONAL */; struct Rel98_AssistanceData_Extension *rel98_AssistanceData_Extension /* OPTIONAL */;
struct Rel5_AssistanceData_Extension *rel5_AssistanceData_Extension /* OPTIONAL */; struct Rel5_AssistanceData_Extension *rel5_AssistanceData_Extension /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} AssistanceData_t; } AssistanceData_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_AssistanceData; extern asn_TYPE_descriptor_t asn_DEF_AssistanceData;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/BCCHCarrier.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* BCCHCarrier */ /* BCCHCarrier */
typedef long BCCHCarrier_t; typedef long BCCHCarrier_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_BCCHCarrier; extern asn_TYPE_descriptor_t asn_DEF_BCCHCarrier;
asn_struct_free_f BCCHCarrier_free; asn_struct_free_f BCCHCarrier_free;
asn_struct_print_f BCCHCarrier_print; asn_struct_print_f BCCHCarrier_print;
asn_constr_check_f BCCHCarrier_constraint; asn_constr_check_f BCCHCarrier_constraint;
ber_type_decoder_f BCCHCarrier_decode_ber; ber_type_decoder_f BCCHCarrier_decode_ber;
der_type_encoder_f BCCHCarrier_encode_der; der_type_encoder_f BCCHCarrier_encode_der;
xer_type_decoder_f BCCHCarrier_decode_xer; xer_type_decoder_f BCCHCarrier_decode_xer;
xer_type_encoder_f BCCHCarrier_encode_xer; xer_type_encoder_f BCCHCarrier_encode_xer;
per_type_decoder_f BCCHCarrier_decode_uper; per_type_decoder_f BCCHCarrier_decode_uper;
per_type_encoder_f BCCHCarrier_encode_uper; per_type_encoder_f BCCHCarrier_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

25
src/core/libs/supl/asn-rrlp/BIT_STRING.h
View File

@ -8,24 +8,25 @@
#include <OCTET_STRING.h> /* Some help from OCTET STRING */ #include <OCTET_STRING.h> /* Some help from OCTET STRING */
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
typedef struct BIT_STRING_s typedef struct BIT_STRING_s
{ {
uint8_t *buf; /* BIT STRING body */ uint8_t *buf; /* BIT STRING body */
int size; /* Size of the above buffer */ int size; /* Size of the above buffer */
int bits_unused; /* Unused trailing bits in the last octet (0..7) */ int bits_unused; /* Unused trailing bits in the last octet (0..7) */
asn_struct_ctx_t _asn_ctx; /* Parsing across buffer boundaries */ asn_struct_ctx_t _asn_ctx; /* Parsing across buffer boundaries */
} BIT_STRING_t; } BIT_STRING_t;
extern asn_TYPE_descriptor_t asn_DEF_BIT_STRING; extern asn_TYPE_descriptor_t asn_DEF_BIT_STRING;
asn_struct_print_f BIT_STRING_print; /* Human-readable output */ asn_struct_print_f BIT_STRING_print; /* Human-readable output */
asn_constr_check_f BIT_STRING_constraint; asn_constr_check_f BIT_STRING_constraint;
xer_type_encoder_f BIT_STRING_encode_xer; xer_type_encoder_f BIT_STRING_encode_xer;
#ifdef __cplusplus #ifdef __cplusplus
} }

25
src/core/libs/supl/asn-rrlp/BOOLEAN.h
View File

@ -8,26 +8,27 @@
#include <asn_application.h> #include <asn_application.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* /*
* The underlying integer may contain various values, but everything * The underlying integer may contain various values, but everything
* non-zero is capped to 0xff by the DER encoder. The BER decoder may * non-zero is capped to 0xff by the DER encoder. The BER decoder may
* yield non-zero values different from 1, beware. * yield non-zero values different from 1, beware.
*/ */
typedef int BOOLEAN_t; typedef int BOOLEAN_t;
extern asn_TYPE_descriptor_t asn_DEF_BOOLEAN; extern asn_TYPE_descriptor_t asn_DEF_BOOLEAN;
asn_struct_free_f BOOLEAN_free; asn_struct_free_f BOOLEAN_free;
asn_struct_print_f BOOLEAN_print; asn_struct_print_f BOOLEAN_print;
ber_type_decoder_f BOOLEAN_decode_ber; ber_type_decoder_f BOOLEAN_decode_ber;
der_type_encoder_f BOOLEAN_encode_der; der_type_encoder_f BOOLEAN_encode_der;
xer_type_decoder_f BOOLEAN_decode_xer; xer_type_decoder_f BOOLEAN_decode_xer;
xer_type_encoder_f BOOLEAN_encode_xer; xer_type_encoder_f BOOLEAN_encode_xer;
per_type_decoder_f BOOLEAN_decode_uper; per_type_decoder_f BOOLEAN_decode_uper;
per_type_encoder_f BOOLEAN_encode_uper; per_type_encoder_f BOOLEAN_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/BSIC.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* BSIC */ /* BSIC */
typedef long BSIC_t; typedef long BSIC_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_BSIC; extern asn_TYPE_descriptor_t asn_DEF_BSIC;
asn_struct_free_f BSIC_free; asn_struct_free_f BSIC_free;
asn_struct_print_f BSIC_print; asn_struct_print_f BSIC_print;
asn_constr_check_f BSIC_constraint; asn_constr_check_f BSIC_constraint;
ber_type_decoder_f BSIC_decode_ber; ber_type_decoder_f BSIC_decode_ber;
der_type_encoder_f BSIC_encode_der; der_type_encoder_f BSIC_encode_der;
xer_type_decoder_f BSIC_decode_xer; xer_type_decoder_f BSIC_decode_xer;
xer_type_encoder_f BSIC_encode_xer; xer_type_encoder_f BSIC_encode_xer;
per_type_decoder_f BSIC_decode_uper; per_type_decoder_f BSIC_decode_uper;
per_type_encoder_f BSIC_encode_uper; per_type_encoder_f BSIC_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/BSICAndCarrier.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* BSICAndCarrier */ /* BSICAndCarrier */
typedef struct BSICAndCarrier typedef struct BSICAndCarrier
{ {
BCCHCarrier_t carrier; BCCHCarrier_t carrier;
BSIC_t bsic; BSIC_t bsic;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} BSICAndCarrier_t; } BSICAndCarrier_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_BSICAndCarrier; extern asn_TYPE_descriptor_t asn_DEF_BSICAndCarrier;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/BTSPosition.h
View File

@ -14,23 +14,24 @@
#include "Ext-GeographicalInformation.h" #include "Ext-GeographicalInformation.h"
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* BTSPosition */ /* BTSPosition */
typedef Ext_GeographicalInformation_t BTSPosition_t; typedef Ext_GeographicalInformation_t BTSPosition_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_BTSPosition; extern asn_TYPE_descriptor_t asn_DEF_BTSPosition;
asn_struct_free_f BTSPosition_free; asn_struct_free_f BTSPosition_free;
asn_struct_print_f BTSPosition_print; asn_struct_print_f BTSPosition_print;
asn_constr_check_f BTSPosition_constraint; asn_constr_check_f BTSPosition_constraint;
ber_type_decoder_f BTSPosition_decode_ber; ber_type_decoder_f BTSPosition_decode_ber;
der_type_encoder_f BTSPosition_encode_der; der_type_encoder_f BTSPosition_encode_der;
xer_type_decoder_f BTSPosition_decode_xer; xer_type_decoder_f BTSPosition_decode_xer;
xer_type_encoder_f BTSPosition_encode_xer; xer_type_encoder_f BTSPosition_encode_xer;
per_type_decoder_f BTSPosition_decode_uper; per_type_decoder_f BTSPosition_decode_uper;
per_type_encoder_f BTSPosition_encode_uper; per_type_encoder_f BTSPosition_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/BadSignalElement.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* BadSignalElement */ /* BadSignalElement */
typedef struct BadSignalElement typedef struct BadSignalElement
{ {
SVID_t badSVID; SVID_t badSVID;
long *badSignalID /* OPTIONAL */; long *badSignalID /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} BadSignalElement_t; } BadSignalElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_BadSignalElement; extern asn_TYPE_descriptor_t asn_DEF_BadSignalElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/BitNumber.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* BitNumber */ /* BitNumber */
typedef long BitNumber_t; typedef long BitNumber_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_BitNumber; extern asn_TYPE_descriptor_t asn_DEF_BitNumber;
asn_struct_free_f BitNumber_free; asn_struct_free_f BitNumber_free;
asn_struct_print_f BitNumber_print; asn_struct_print_f BitNumber_print;
asn_constr_check_f BitNumber_constraint; asn_constr_check_f BitNumber_constraint;
ber_type_decoder_f BitNumber_decode_ber; ber_type_decoder_f BitNumber_decode_ber;
der_type_encoder_f BitNumber_encode_der; der_type_encoder_f BitNumber_encode_der;
xer_type_decoder_f BitNumber_decode_xer; xer_type_decoder_f BitNumber_decode_xer;
xer_type_encoder_f BitNumber_encode_xer; xer_type_encoder_f BitNumber_encode_xer;
per_type_decoder_f BitNumber_decode_uper; per_type_decoder_f BitNumber_decode_uper;
per_type_encoder_f BitNumber_encode_uper; per_type_encoder_f BitNumber_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/CalcAssistanceBTS.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* CalcAssistanceBTS */ /* CalcAssistanceBTS */
typedef struct CalcAssistanceBTS typedef struct CalcAssistanceBTS
{ {
FineRTD_t fineRTD; FineRTD_t fineRTD;
ReferenceWGS84_t referenceWGS84; ReferenceWGS84_t referenceWGS84;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} CalcAssistanceBTS_t; } CalcAssistanceBTS_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_CalcAssistanceBTS; extern asn_TYPE_descriptor_t asn_DEF_CalcAssistanceBTS;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/CellID.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* CellID */ /* CellID */
typedef long CellID_t; typedef long CellID_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_CellID; extern asn_TYPE_descriptor_t asn_DEF_CellID;
asn_struct_free_f CellID_free; asn_struct_free_f CellID_free;
asn_struct_print_f CellID_print; asn_struct_print_f CellID_print;
asn_constr_check_f CellID_constraint; asn_constr_check_f CellID_constraint;
ber_type_decoder_f CellID_decode_ber; ber_type_decoder_f CellID_decode_ber;
der_type_encoder_f CellID_encode_der; der_type_encoder_f CellID_encode_der;
xer_type_decoder_f CellID_decode_xer; xer_type_decoder_f CellID_decode_xer;
xer_type_encoder_f CellID_encode_xer; xer_type_encoder_f CellID_encode_xer;
per_type_decoder_f CellID_decode_uper; per_type_decoder_f CellID_decode_uper;
per_type_encoder_f CellID_encode_uper; per_type_encoder_f CellID_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/CellIDAndLAC.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* CellIDAndLAC */ /* CellIDAndLAC */
typedef struct CellIDAndLAC typedef struct CellIDAndLAC
{ {
LAC_t referenceLAC; LAC_t referenceLAC;
CellID_t referenceCI; CellID_t referenceCI;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} CellIDAndLAC_t; } CellIDAndLAC_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_CellIDAndLAC; extern asn_TYPE_descriptor_t asn_DEF_CellIDAndLAC;
#ifdef __cplusplus #ifdef __cplusplus
} }

57
src/core/libs/supl/asn-rrlp/ControlHeader.h
View File

@ -14,39 +14,40 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct ReferenceTime; struct ReferenceTime;
struct RefLocation; struct RefLocation;
struct DGPSCorrections; struct DGPSCorrections;
struct NavigationModel; struct NavigationModel;
struct IonosphericModel; struct IonosphericModel;
struct UTCModel; struct UTCModel;
struct Almanac; struct Almanac;
struct AcquisAssist; struct AcquisAssist;
struct SeqOf_BadSatelliteSet; struct SeqOf_BadSatelliteSet;
/* ControlHeader */ /* ControlHeader */
typedef struct ControlHeader typedef struct ControlHeader
{ {
struct ReferenceTime *referenceTime /* OPTIONAL */; struct ReferenceTime *referenceTime /* OPTIONAL */;
struct RefLocation *refLocation /* OPTIONAL */; struct RefLocation *refLocation /* OPTIONAL */;
struct DGPSCorrections *dgpsCorrections /* OPTIONAL */; struct DGPSCorrections *dgpsCorrections /* OPTIONAL */;
struct NavigationModel *navigationModel /* OPTIONAL */; struct NavigationModel *navigationModel /* OPTIONAL */;
struct IonosphericModel *ionosphericModel /* OPTIONAL */; struct IonosphericModel *ionosphericModel /* OPTIONAL */;
struct UTCModel *utcModel /* OPTIONAL */; struct UTCModel *utcModel /* OPTIONAL */;
struct Almanac *almanac /* OPTIONAL */; struct Almanac *almanac /* OPTIONAL */;
struct AcquisAssist *acquisAssist /* OPTIONAL */; struct AcquisAssist *acquisAssist /* OPTIONAL */;
struct SeqOf_BadSatelliteSet *realTimeIntegrity /* OPTIONAL */; struct SeqOf_BadSatelliteSet *realTimeIntegrity /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} ControlHeader_t; } ControlHeader_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_ControlHeader; extern asn_TYPE_descriptor_t asn_DEF_ControlHeader;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/DGANSSSgnElement.h
View File

@ -16,24 +16,25 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* DGANSSSgnElement */ /* DGANSSSgnElement */
typedef struct DGANSSSgnElement typedef struct DGANSSSgnElement
{ {
SVID_t svID; SVID_t svID;
long iod; long iod;
long udre; long udre;
long pseudoRangeCor; long pseudoRangeCor;
long rangeRateCor; long rangeRateCor;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} DGANSSSgnElement_t; } DGANSSSgnElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_DGANSSSgnElement; extern asn_TYPE_descriptor_t asn_DEF_DGANSSSgnElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

25
src/core/libs/supl/asn-rrlp/DGPSCorrections.h
View File

@ -16,22 +16,23 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* DGPSCorrections */ /* DGPSCorrections */
typedef struct DGPSCorrections typedef struct DGPSCorrections
{ {
long gpsTOW; long gpsTOW;
long status; long status;
SeqOfSatElement_t satList; SeqOfSatElement_t satList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} DGPSCorrections_t; } DGPSCorrections_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_DGPSCorrections; extern asn_TYPE_descriptor_t asn_DEF_DGPSCorrections;
#ifdef __cplusplus #ifdef __cplusplus
} }

11
src/core/libs/supl/asn-rrlp/ENUMERATED.h
View File

@ -8,15 +8,16 @@
#include <INTEGER.h> #include <INTEGER.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
typedef INTEGER_t ENUMERATED_t; /* Implemented via INTEGER */ typedef INTEGER_t ENUMERATED_t; /* Implemented via INTEGER */
extern asn_TYPE_descriptor_t asn_DEF_ENUMERATED; extern asn_TYPE_descriptor_t asn_DEF_ENUMERATED;
per_type_decoder_f ENUMERATED_decode_uper; per_type_decoder_f ENUMERATED_decode_uper;
per_type_encoder_f ENUMERATED_encode_uper; per_type_encoder_f ENUMERATED_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/EOTDQuality.h
View File

@ -15,21 +15,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* EOTDQuality */ /* EOTDQuality */
typedef struct EOTDQuality typedef struct EOTDQuality
{ {
long nbrOfMeasurements; long nbrOfMeasurements;
long stdOfEOTD; long stdOfEOTD;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} EOTDQuality_t; } EOTDQuality_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_EOTDQuality; extern asn_TYPE_descriptor_t asn_DEF_EOTDQuality;
#ifdef __cplusplus #ifdef __cplusplus
} }

44
src/core/libs/supl/asn-rrlp/EnvironmentCharacter.h
View File

@ -14,33 +14,35 @@
#include <ENUMERATED.h> #include <ENUMERATED.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum EnvironmentCharacter { typedef enum EnvironmentCharacter
EnvironmentCharacter_badArea = 0, {
EnvironmentCharacter_notBadArea = 1, EnvironmentCharacter_badArea = 0,
EnvironmentCharacter_mixedArea = 2 EnvironmentCharacter_notBadArea = 1,
/* EnvironmentCharacter_mixedArea = 2
/*
* Enumeration is extensible * Enumeration is extensible
*/ */
} e_EnvironmentCharacter; } e_EnvironmentCharacter;
/* EnvironmentCharacter */ /* EnvironmentCharacter */
typedef ENUMERATED_t EnvironmentCharacter_t; typedef ENUMERATED_t EnvironmentCharacter_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_EnvironmentCharacter; extern asn_TYPE_descriptor_t asn_DEF_EnvironmentCharacter;
asn_struct_free_f EnvironmentCharacter_free; asn_struct_free_f EnvironmentCharacter_free;
asn_struct_print_f EnvironmentCharacter_print; asn_struct_print_f EnvironmentCharacter_print;
asn_constr_check_f EnvironmentCharacter_constraint; asn_constr_check_f EnvironmentCharacter_constraint;
ber_type_decoder_f EnvironmentCharacter_decode_ber; ber_type_decoder_f EnvironmentCharacter_decode_ber;
der_type_encoder_f EnvironmentCharacter_encode_der; der_type_encoder_f EnvironmentCharacter_encode_der;
xer_type_decoder_f EnvironmentCharacter_decode_xer; xer_type_decoder_f EnvironmentCharacter_decode_xer;
xer_type_encoder_f EnvironmentCharacter_encode_xer; xer_type_encoder_f EnvironmentCharacter_encode_xer;
per_type_decoder_f EnvironmentCharacter_decode_uper; per_type_decoder_f EnvironmentCharacter_decode_uper;
per_type_encoder_f EnvironmentCharacter_encode_uper; per_type_encoder_f EnvironmentCharacter_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

27
src/core/libs/supl/asn-rrlp/EphemerisSubframe1Reserved.h
View File

@ -15,23 +15,24 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* EphemerisSubframe1Reserved */ /* EphemerisSubframe1Reserved */
typedef struct EphemerisSubframe1Reserved typedef struct EphemerisSubframe1Reserved
{ {
long reserved1; long reserved1;
long reserved2; long reserved2;
long reserved3; long reserved3;
long reserved4; long reserved4;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} EphemerisSubframe1Reserved_t; } EphemerisSubframe1Reserved_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_EphemerisSubframe1Reserved; extern asn_TYPE_descriptor_t asn_DEF_EphemerisSubframe1Reserved;
#ifdef __cplusplus #ifdef __cplusplus
} }

50
src/core/libs/supl/asn-rrlp/ErrorCodes.h
View File

@ -14,36 +14,38 @@
#include <ENUMERATED.h> #include <ENUMERATED.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum ErrorCodes { typedef enum ErrorCodes
ErrorCodes_unDefined = 0, {
ErrorCodes_missingComponet = 1, ErrorCodes_unDefined = 0,
ErrorCodes_incorrectData = 2, ErrorCodes_missingComponet = 1,
ErrorCodes_missingIEorComponentElement = 3, ErrorCodes_incorrectData = 2,
ErrorCodes_messageTooShort = 4, ErrorCodes_missingIEorComponentElement = 3,
ErrorCodes_unknowReferenceNumber = 5 ErrorCodes_messageTooShort = 4,
/* ErrorCodes_unknowReferenceNumber = 5
/*
* Enumeration is extensible * Enumeration is extensible
*/ */
} e_ErrorCodes; } e_ErrorCodes;
/* ErrorCodes */ /* ErrorCodes */
typedef ENUMERATED_t ErrorCodes_t; typedef ENUMERATED_t ErrorCodes_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_ErrorCodes; extern asn_TYPE_descriptor_t asn_DEF_ErrorCodes;
asn_struct_free_f ErrorCodes_free; asn_struct_free_f ErrorCodes_free;
asn_struct_print_f ErrorCodes_print; asn_struct_print_f ErrorCodes_print;
asn_constr_check_f ErrorCodes_constraint; asn_constr_check_f ErrorCodes_constraint;
ber_type_decoder_f ErrorCodes_decode_ber; ber_type_decoder_f ErrorCodes_decode_ber;
der_type_encoder_f ErrorCodes_encode_der; der_type_encoder_f ErrorCodes_encode_der;
xer_type_decoder_f ErrorCodes_decode_xer; xer_type_decoder_f ErrorCodes_decode_xer;
xer_type_encoder_f ErrorCodes_encode_xer; xer_type_encoder_f ErrorCodes_encode_xer;
per_type_decoder_f ErrorCodes_decode_uper; per_type_decoder_f ErrorCodes_decode_uper;
per_type_encoder_f ErrorCodes_encode_uper; per_type_encoder_f ErrorCodes_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/ExpOTDUncertainty.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* ExpOTDUncertainty */ /* ExpOTDUncertainty */
typedef long ExpOTDUncertainty_t; typedef long ExpOTDUncertainty_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_ExpOTDUncertainty; extern asn_TYPE_descriptor_t asn_DEF_ExpOTDUncertainty;
asn_struct_free_f ExpOTDUncertainty_free; asn_struct_free_f ExpOTDUncertainty_free;
asn_struct_print_f ExpOTDUncertainty_print; asn_struct_print_f ExpOTDUncertainty_print;
asn_constr_check_f ExpOTDUncertainty_constraint; asn_constr_check_f ExpOTDUncertainty_constraint;
ber_type_decoder_f ExpOTDUncertainty_decode_ber; ber_type_decoder_f ExpOTDUncertainty_decode_ber;
der_type_encoder_f ExpOTDUncertainty_encode_der; der_type_encoder_f ExpOTDUncertainty_encode_der;
xer_type_decoder_f ExpOTDUncertainty_decode_xer; xer_type_decoder_f ExpOTDUncertainty_decode_xer;
xer_type_encoder_f ExpOTDUncertainty_encode_xer; xer_type_encoder_f ExpOTDUncertainty_encode_xer;
per_type_decoder_f ExpOTDUncertainty_decode_uper; per_type_decoder_f ExpOTDUncertainty_decode_uper;
per_type_encoder_f ExpOTDUncertainty_encode_uper; per_type_encoder_f ExpOTDUncertainty_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/ExpectedOTD.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* ExpectedOTD */ /* ExpectedOTD */
typedef long ExpectedOTD_t; typedef long ExpectedOTD_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_ExpectedOTD; extern asn_TYPE_descriptor_t asn_DEF_ExpectedOTD;
asn_struct_free_f ExpectedOTD_free; asn_struct_free_f ExpectedOTD_free;
asn_struct_print_f ExpectedOTD_print; asn_struct_print_f ExpectedOTD_print;
asn_constr_check_f ExpectedOTD_constraint; asn_constr_check_f ExpectedOTD_constraint;
ber_type_decoder_f ExpectedOTD_decode_ber; ber_type_decoder_f ExpectedOTD_decode_ber;
der_type_encoder_f ExpectedOTD_encode_der; der_type_encoder_f ExpectedOTD_encode_der;
xer_type_decoder_f ExpectedOTD_decode_xer; xer_type_decoder_f ExpectedOTD_decode_xer;
xer_type_encoder_f ExpectedOTD_encode_xer; xer_type_encoder_f ExpectedOTD_encode_xer;
per_type_decoder_f ExpectedOTD_decode_uper; per_type_decoder_f ExpectedOTD_decode_uper;
per_type_encoder_f ExpectedOTD_encode_uper; per_type_encoder_f ExpectedOTD_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/Ext-GeographicalInformation.h
View File

@ -14,23 +14,24 @@
#include <OCTET_STRING.h> #include <OCTET_STRING.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Ext-GeographicalInformation */ /* Ext-GeographicalInformation */
typedef OCTET_STRING_t Ext_GeographicalInformation_t; typedef OCTET_STRING_t Ext_GeographicalInformation_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_Ext_GeographicalInformation; extern asn_TYPE_descriptor_t asn_DEF_Ext_GeographicalInformation;
asn_struct_free_f Ext_GeographicalInformation_free; asn_struct_free_f Ext_GeographicalInformation_free;
asn_struct_print_f Ext_GeographicalInformation_print; asn_struct_print_f Ext_GeographicalInformation_print;
asn_constr_check_f Ext_GeographicalInformation_constraint; asn_constr_check_f Ext_GeographicalInformation_constraint;
ber_type_decoder_f Ext_GeographicalInformation_decode_ber; ber_type_decoder_f Ext_GeographicalInformation_decode_ber;
der_type_encoder_f Ext_GeographicalInformation_encode_der; der_type_encoder_f Ext_GeographicalInformation_encode_der;
xer_type_decoder_f Ext_GeographicalInformation_decode_xer; xer_type_decoder_f Ext_GeographicalInformation_decode_xer;
xer_type_encoder_f Ext_GeographicalInformation_encode_xer; xer_type_encoder_f Ext_GeographicalInformation_encode_xer;
per_type_decoder_f Ext_GeographicalInformation_decode_uper; per_type_decoder_f Ext_GeographicalInformation_decode_uper;
per_type_encoder_f Ext_GeographicalInformation_encode_uper; per_type_encoder_f Ext_GeographicalInformation_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/Extended-reference.h
View File

@ -15,21 +15,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Extended-reference */ /* Extended-reference */
typedef struct Extended_reference typedef struct Extended_reference
{ {
long smlc_code; long smlc_code;
long transaction_ID; long transaction_ID;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} Extended_reference_t; } Extended_reference_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_Extended_reference; extern asn_TYPE_descriptor_t asn_DEF_Extended_reference;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/ExtensionContainer.h
View File

@ -14,23 +14,24 @@
#include <INTEGER.h> #include <INTEGER.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* ExtensionContainer */ /* ExtensionContainer */
typedef INTEGER_t ExtensionContainer_t; typedef INTEGER_t ExtensionContainer_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_ExtensionContainer; extern asn_TYPE_descriptor_t asn_DEF_ExtensionContainer;
asn_struct_free_f ExtensionContainer_free; asn_struct_free_f ExtensionContainer_free;
asn_struct_print_f ExtensionContainer_print; asn_struct_print_f ExtensionContainer_print;
asn_constr_check_f ExtensionContainer_constraint; asn_constr_check_f ExtensionContainer_constraint;
ber_type_decoder_f ExtensionContainer_decode_ber; ber_type_decoder_f ExtensionContainer_decode_ber;
der_type_encoder_f ExtensionContainer_encode_der; der_type_encoder_f ExtensionContainer_encode_der;
xer_type_decoder_f ExtensionContainer_decode_xer; xer_type_decoder_f ExtensionContainer_decode_xer;
xer_type_encoder_f ExtensionContainer_encode_xer; xer_type_encoder_f ExtensionContainer_encode_xer;
per_type_decoder_f ExtensionContainer_decode_uper; per_type_decoder_f ExtensionContainer_decode_uper;
per_type_encoder_f ExtensionContainer_encode_uper; per_type_encoder_f ExtensionContainer_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/FineRTD.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* FineRTD */ /* FineRTD */
typedef long FineRTD_t; typedef long FineRTD_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_FineRTD; extern asn_TYPE_descriptor_t asn_DEF_FineRTD;
asn_struct_free_f FineRTD_free; asn_struct_free_f FineRTD_free;
asn_struct_print_f FineRTD_print; asn_struct_print_f FineRTD_print;
asn_constr_check_f FineRTD_constraint; asn_constr_check_f FineRTD_constraint;
ber_type_decoder_f FineRTD_decode_ber; ber_type_decoder_f FineRTD_decode_ber;
der_type_encoder_f FineRTD_encode_der; der_type_encoder_f FineRTD_encode_der;
xer_type_decoder_f FineRTD_decode_xer; xer_type_decoder_f FineRTD_decode_xer;
xer_type_encoder_f FineRTD_encode_xer; xer_type_encoder_f FineRTD_encode_xer;
per_type_decoder_f FineRTD_decode_uper; per_type_decoder_f FineRTD_decode_uper;
per_type_encoder_f FineRTD_encode_uper; per_type_encoder_f FineRTD_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

40
src/core/libs/supl/asn-rrlp/FixType.h
View File

@ -14,29 +14,31 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum FixType { typedef enum FixType
FixType_twoDFix = 0, {
FixType_threeDFix = 1 FixType_twoDFix = 0,
} e_FixType; FixType_threeDFix = 1
} e_FixType;
/* FixType */ /* FixType */
typedef long FixType_t; typedef long FixType_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_FixType; extern asn_TYPE_descriptor_t asn_DEF_FixType;
asn_struct_free_f FixType_free; asn_struct_free_f FixType_free;
asn_struct_print_f FixType_print; asn_struct_print_f FixType_print;
asn_constr_check_f FixType_constraint; asn_constr_check_f FixType_constraint;
ber_type_decoder_f FixType_decode_ber; ber_type_decoder_f FixType_decode_ber;
der_type_encoder_f FixType_encode_der; der_type_encoder_f FixType_encode_der;
xer_type_decoder_f FixType_decode_xer; xer_type_decoder_f FixType_decode_xer;
xer_type_encoder_f FixType_encode_xer; xer_type_encoder_f FixType_encode_xer;
per_type_decoder_f FixType_decode_uper; per_type_decoder_f FixType_decode_uper;
per_type_encoder_f FixType_encode_uper; per_type_encoder_f FixType_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/FrameDrift.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* FrameDrift */ /* FrameDrift */
typedef long FrameDrift_t; typedef long FrameDrift_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_FrameDrift; extern asn_TYPE_descriptor_t asn_DEF_FrameDrift;
asn_struct_free_f FrameDrift_free; asn_struct_free_f FrameDrift_free;
asn_struct_print_f FrameDrift_print; asn_struct_print_f FrameDrift_print;
asn_constr_check_f FrameDrift_constraint; asn_constr_check_f FrameDrift_constraint;
ber_type_decoder_f FrameDrift_decode_ber; ber_type_decoder_f FrameDrift_decode_ber;
der_type_encoder_f FrameDrift_encode_der; der_type_encoder_f FrameDrift_encode_der;
xer_type_decoder_f FrameDrift_decode_xer; xer_type_decoder_f FrameDrift_decode_xer;
xer_type_encoder_f FrameDrift_encode_xer; xer_type_encoder_f FrameDrift_encode_xer;
per_type_decoder_f FrameDrift_decode_uper; per_type_decoder_f FrameDrift_decode_uper;
per_type_encoder_f FrameDrift_encode_uper; per_type_encoder_f FrameDrift_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/FrameNumber.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* FrameNumber */ /* FrameNumber */
typedef long FrameNumber_t; typedef long FrameNumber_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_FrameNumber; extern asn_TYPE_descriptor_t asn_DEF_FrameNumber;
asn_struct_free_f FrameNumber_free; asn_struct_free_f FrameNumber_free;
asn_struct_print_f FrameNumber_print; asn_struct_print_f FrameNumber_print;
asn_constr_check_f FrameNumber_constraint; asn_constr_check_f FrameNumber_constraint;
ber_type_decoder_f FrameNumber_decode_ber; ber_type_decoder_f FrameNumber_decode_ber;
der_type_encoder_f FrameNumber_encode_der; der_type_encoder_f FrameNumber_encode_der;
xer_type_decoder_f FrameNumber_decode_xer; xer_type_decoder_f FrameNumber_decode_xer;
xer_type_encoder_f FrameNumber_encode_xer; xer_type_encoder_f FrameNumber_encode_xer;
per_type_decoder_f FrameNumber_decode_uper; per_type_decoder_f FrameNumber_decode_uper;
per_type_encoder_f FrameNumber_encode_uper; per_type_encoder_f FrameNumber_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

21
src/core/libs/supl/asn-rrlp/GANSS-AssistData.h
View File

@ -15,20 +15,21 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSS-AssistData */ /* GANSS-AssistData */
typedef struct GANSS_AssistData typedef struct GANSS_AssistData
{ {
GANSS_ControlHeader_t ganss_controlHeader; GANSS_ControlHeader_t ganss_controlHeader;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSS_AssistData_t; } GANSS_AssistData_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSS_AssistData; extern asn_TYPE_descriptor_t asn_DEF_GANSS_AssistData;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSS-ControlHeader.h
View File

@ -14,25 +14,26 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct GANSSCommonAssistData; struct GANSSCommonAssistData;
struct SeqOfGANSSGenericAssistDataElement; struct SeqOfGANSSGenericAssistDataElement;
/* GANSS-ControlHeader */ /* GANSS-ControlHeader */
typedef struct GANSS_ControlHeader typedef struct GANSS_ControlHeader
{ {
struct GANSSCommonAssistData *ganssCommonAssistData /* OPTIONAL */; struct GANSSCommonAssistData *ganssCommonAssistData /* OPTIONAL */;
struct SeqOfGANSSGenericAssistDataElement *ganssGenericAssistDataList /* OPTIONAL */; struct SeqOfGANSSGenericAssistDataElement *ganssGenericAssistDataList /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSS_ControlHeader_t; } GANSS_ControlHeader_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSS_ControlHeader; extern asn_TYPE_descriptor_t asn_DEF_GANSS_ControlHeader;
#ifdef __cplusplus #ifdef __cplusplus
} }

33
src/core/libs/supl/asn-rrlp/GANSS-MsrSetElement.h
View File

@ -18,27 +18,28 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct ReferenceFrame; struct ReferenceFrame;
/* GANSS-MsrSetElement */ /* GANSS-MsrSetElement */
typedef struct GANSS_MsrSetElement typedef struct GANSS_MsrSetElement
{ {
struct ReferenceFrame *referenceFrame /* OPTIONAL */; struct ReferenceFrame *referenceFrame /* OPTIONAL */;
GANSSTODm_t *ganssTODm /* OPTIONAL */; GANSSTODm_t *ganssTODm /* OPTIONAL */;
long *deltaGNASSTOD /* OPTIONAL */; long *deltaGNASSTOD /* OPTIONAL */;
GANSSTODUncertainty_t *ganssTODUncertainty /* OPTIONAL */; GANSSTODUncertainty_t *ganssTODUncertainty /* OPTIONAL */;
SeqOfGANSS_SgnTypeElement_t ganss_SgnTypeList; SeqOfGANSS_SgnTypeElement_t ganss_SgnTypeList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSS_MsrSetElement_t; } GANSS_MsrSetElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSS_MsrSetElement; extern asn_TYPE_descriptor_t asn_DEF_GANSS_MsrSetElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

37
src/core/libs/supl/asn-rrlp/GANSS-SgnElement.h
View File

@ -17,28 +17,29 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSS-SgnElement */ /* GANSS-SgnElement */
typedef struct GANSS_SgnElement typedef struct GANSS_SgnElement
{ {
SVID_t svID; SVID_t svID;
long cNo; long cNo;
MpathIndic_t mpathDet; MpathIndic_t mpathDet;
long *carrierQualityInd /* OPTIONAL */; long *carrierQualityInd /* OPTIONAL */;
long codePhase; long codePhase;
long *integerCodePhase /* OPTIONAL */; long *integerCodePhase /* OPTIONAL */;
long codePhaseRMSError; long codePhaseRMSError;
long *doppler /* OPTIONAL */; long *doppler /* OPTIONAL */;
long *adr /* OPTIONAL */; long *adr /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSS_SgnElement_t; } GANSS_SgnElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSS_SgnElement; extern asn_TYPE_descriptor_t asn_DEF_GANSS_SgnElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/GANSS-SgnTypeElement.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSS-SgnTypeElement */ /* GANSS-SgnTypeElement */
typedef struct GANSS_SgnTypeElement typedef struct GANSS_SgnTypeElement
{ {
long ganssSignalID; long ganssSignalID;
SeqOfGANSS_SgnElement_t ganss_SgnList; SeqOfGANSS_SgnElement_t ganss_SgnList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSS_SgnTypeElement_t; } GANSS_SgnTypeElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSS_SgnTypeElement; extern asn_TYPE_descriptor_t asn_DEF_GANSS_SgnTypeElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

46
src/core/libs/supl/asn-rrlp/GANSSAlmanacElement.h
View File

@ -15,36 +15,38 @@
#include <constr_CHOICE.h> #include <constr_CHOICE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum GANSSAlmanacElement_PR { typedef enum GANSSAlmanacElement_PR
GANSSAlmanacElement_PR_NOTHING, /* No components present */
GANSSAlmanacElement_PR_keplerianAlmanacSet,
/* Extensions may appear below */
} GANSSAlmanacElement_PR;
/* GANSSAlmanacElement */
typedef struct GANSSAlmanacElement
{
GANSSAlmanacElement_PR present;
union GANSSAlmanacElement_u
{ {
Almanac_KeplerianSet_t keplerianAlmanacSet; GANSSAlmanacElement_PR_NOTHING, /* No components present */
/* GANSSAlmanacElement_PR_keplerianAlmanacSet,
/* Extensions may appear below */
} GANSSAlmanacElement_PR;
/* GANSSAlmanacElement */
typedef struct GANSSAlmanacElement
{
GANSSAlmanacElement_PR present;
union GANSSAlmanacElement_u
{
Almanac_KeplerianSet_t keplerianAlmanacSet;
/*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
} choice; } choice;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSAlmanacElement_t; } GANSSAlmanacElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSAlmanacElement; extern asn_TYPE_descriptor_t asn_DEF_GANSSAlmanacElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSSAlmanacModel.h
View File

@ -17,24 +17,25 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSAlmanacModel */ /* GANSSAlmanacModel */
typedef struct GANSSAlmanacModel typedef struct GANSSAlmanacModel
{ {
long weekNumber; long weekNumber;
SVIDMASK_t svIDMask; SVIDMASK_t svIDMask;
long *toa /* OPTIONAL */; long *toa /* OPTIONAL */;
long *ioda /* OPTIONAL */; long *ioda /* OPTIONAL */;
SeqOfGANSSAlmanacElement_t ganssAlmanacList; SeqOfGANSSAlmanacElement_t ganssAlmanacList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSAlmanacModel_t; } GANSSAlmanacModel_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSAlmanacModel; extern asn_TYPE_descriptor_t asn_DEF_GANSSAlmanacModel;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSSAssistanceData.h
View File

@ -14,23 +14,24 @@
#include <OCTET_STRING.h> #include <OCTET_STRING.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSAssistanceData */ /* GANSSAssistanceData */
typedef OCTET_STRING_t GANSSAssistanceData_t; typedef OCTET_STRING_t GANSSAssistanceData_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSAssistanceData; extern asn_TYPE_descriptor_t asn_DEF_GANSSAssistanceData;
asn_struct_free_f GANSSAssistanceData_free; asn_struct_free_f GANSSAssistanceData_free;
asn_struct_print_f GANSSAssistanceData_print; asn_struct_print_f GANSSAssistanceData_print;
asn_constr_check_f GANSSAssistanceData_constraint; asn_constr_check_f GANSSAssistanceData_constraint;
ber_type_decoder_f GANSSAssistanceData_decode_ber; ber_type_decoder_f GANSSAssistanceData_decode_ber;
der_type_encoder_f GANSSAssistanceData_encode_der; der_type_encoder_f GANSSAssistanceData_encode_der;
xer_type_decoder_f GANSSAssistanceData_decode_xer; xer_type_decoder_f GANSSAssistanceData_decode_xer;
xer_type_encoder_f GANSSAssistanceData_encode_xer; xer_type_encoder_f GANSSAssistanceData_encode_xer;
per_type_decoder_f GANSSAssistanceData_decode_uper; per_type_decoder_f GANSSAssistanceData_decode_uper;
per_type_encoder_f GANSSAssistanceData_encode_uper; per_type_encoder_f GANSSAssistanceData_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

46
src/core/libs/supl/asn-rrlp/GANSSClockModel.h
View File

@ -15,36 +15,38 @@
#include <constr_CHOICE.h> #include <constr_CHOICE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum GANSSClockModel_PR { typedef enum GANSSClockModel_PR
GANSSClockModel_PR_NOTHING, /* No components present */
GANSSClockModel_PR_standardClockModelList,
/* Extensions may appear below */
} GANSSClockModel_PR;
/* GANSSClockModel */
typedef struct GANSSClockModel
{
GANSSClockModel_PR present;
union GANSSClockModel_u
{ {
SeqOfStandardClockModelElement_t standardClockModelList; GANSSClockModel_PR_NOTHING, /* No components present */
/* GANSSClockModel_PR_standardClockModelList,
/* Extensions may appear below */
} GANSSClockModel_PR;
/* GANSSClockModel */
typedef struct GANSSClockModel
{
GANSSClockModel_PR present;
union GANSSClockModel_u
{
SeqOfStandardClockModelElement_t standardClockModelList;
/*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
} choice; } choice;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSClockModel_t; } GANSSClockModel_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSClockModel; extern asn_TYPE_descriptor_t asn_DEF_GANSSClockModel;
#ifdef __cplusplus #ifdef __cplusplus
} }

35
src/core/libs/supl/asn-rrlp/GANSSCommonAssistData.h
View File

@ -14,31 +14,32 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct GANSSReferenceTime; struct GANSSReferenceTime;
struct GANSSRefLocation; struct GANSSRefLocation;
struct GANSSIonosphericModel; struct GANSSIonosphericModel;
/* GANSSCommonAssistData */ /* GANSSCommonAssistData */
typedef struct GANSSCommonAssistData typedef struct GANSSCommonAssistData
{ {
struct GANSSReferenceTime *ganssReferenceTime /* OPTIONAL */; struct GANSSReferenceTime *ganssReferenceTime /* OPTIONAL */;
struct GANSSRefLocation *ganssRefLocation /* OPTIONAL */; struct GANSSRefLocation *ganssRefLocation /* OPTIONAL */;
struct GANSSIonosphericModel *ganssIonosphericModel /* OPTIONAL */; struct GANSSIonosphericModel *ganssIonosphericModel /* OPTIONAL */;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSCommonAssistData_t; } GANSSCommonAssistData_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSCommonAssistData; extern asn_TYPE_descriptor_t asn_DEF_GANSSCommonAssistData;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSSDataBit.h
View File

@ -14,23 +14,24 @@
#include <NativeInteger.h> #include <NativeInteger.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSDataBit */ /* GANSSDataBit */
typedef long GANSSDataBit_t; typedef long GANSSDataBit_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSDataBit; extern asn_TYPE_descriptor_t asn_DEF_GANSSDataBit;
asn_struct_free_f GANSSDataBit_free; asn_struct_free_f GANSSDataBit_free;
asn_struct_print_f GANSSDataBit_print; asn_struct_print_f GANSSDataBit_print;
asn_constr_check_f GANSSDataBit_constraint; asn_constr_check_f GANSSDataBit_constraint;
ber_type_decoder_f GANSSDataBit_decode_ber; ber_type_decoder_f GANSSDataBit_decode_ber;
der_type_encoder_f GANSSDataBit_encode_der; der_type_encoder_f GANSSDataBit_encode_der;
xer_type_decoder_f GANSSDataBit_decode_xer; xer_type_decoder_f GANSSDataBit_decode_xer;
xer_type_encoder_f GANSSDataBit_encode_xer; xer_type_encoder_f GANSSDataBit_encode_xer;
per_type_decoder_f GANSSDataBit_decode_uper; per_type_decoder_f GANSSDataBit_decode_uper;
per_type_encoder_f GANSSDataBit_encode_uper; per_type_encoder_f GANSSDataBit_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

27
src/core/libs/supl/asn-rrlp/GANSSDataBitAssist.h
View File

@ -17,23 +17,24 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSDataBitAssist */ /* GANSSDataBitAssist */
typedef struct GANSSDataBitAssist typedef struct GANSSDataBitAssist
{ {
long ganssTOD; long ganssTOD;
SVID_t svID; SVID_t svID;
long ganssDataTypeID; long ganssDataTypeID;
SeqOf_GANSSDataBits_t ganssDataBits; SeqOf_GANSSDataBits_t ganssDataBits;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSDataBitAssist_t; } GANSSDataBitAssist_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSDataBitAssist; extern asn_TYPE_descriptor_t asn_DEF_GANSSDataBitAssist;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/GANSSDiffCorrections.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSDiffCorrections */ /* GANSSDiffCorrections */
typedef struct GANSSDiffCorrections typedef struct GANSSDiffCorrections
{ {
long dganssRefTime; long dganssRefTime;
SeqOfSgnTypeElement_t sgnTypeList; SeqOfSgnTypeElement_t sgnTypeList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSDiffCorrections_t; } GANSSDiffCorrections_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSDiffCorrections; extern asn_TYPE_descriptor_t asn_DEF_GANSSDiffCorrections;
#ifdef __cplusplus #ifdef __cplusplus
} }

57
src/core/libs/supl/asn-rrlp/GANSSGenericAssistDataElement.h
View File

@ -15,42 +15,43 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct SeqOfGANSSTimeModel; struct SeqOfGANSSTimeModel;
struct GANSSDiffCorrections; struct GANSSDiffCorrections;
struct GANSSNavModel; struct GANSSNavModel;
struct GANSSRealTimeIntegrity; struct GANSSRealTimeIntegrity;
struct GANSSDataBitAssist; struct GANSSDataBitAssist;
struct GANSSRefMeasurementAssist; struct GANSSRefMeasurementAssist;
struct GANSSAlmanacModel; struct GANSSAlmanacModel;
struct GANSSUTCModel; struct GANSSUTCModel;
/* GANSSGenericAssistDataElement */ /* GANSSGenericAssistDataElement */
typedef struct GANSSGenericAssistDataElement typedef struct GANSSGenericAssistDataElement
{ {
long *ganssID /* OPTIONAL */; long *ganssID /* OPTIONAL */;
struct SeqOfGANSSTimeModel *ganssTimeModel /* OPTIONAL */; struct SeqOfGANSSTimeModel *ganssTimeModel /* OPTIONAL */;
struct GANSSDiffCorrections *ganssDiffCorrections /* OPTIONAL */; struct GANSSDiffCorrections *ganssDiffCorrections /* OPTIONAL */;
struct GANSSNavModel *ganssNavigationModel /* OPTIONAL */; struct GANSSNavModel *ganssNavigationModel /* OPTIONAL */;
struct GANSSRealTimeIntegrity *ganssRealTimeIntegrity /* OPTIONAL */; struct GANSSRealTimeIntegrity *ganssRealTimeIntegrity /* OPTIONAL */;
struct GANSSDataBitAssist *ganssDataBitAssist /* OPTIONAL */; struct GANSSDataBitAssist *ganssDataBitAssist /* OPTIONAL */;
struct GANSSRefMeasurementAssist *ganssRefMeasurementAssist /* OPTIONAL */; struct GANSSRefMeasurementAssist *ganssRefMeasurementAssist /* OPTIONAL */;
struct GANSSAlmanacModel *ganssAlmanacModel /* OPTIONAL */; struct GANSSAlmanacModel *ganssAlmanacModel /* OPTIONAL */;
struct GANSSUTCModel *ganssUTCModel /* OPTIONAL */; struct GANSSUTCModel *ganssUTCModel /* OPTIONAL */;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSGenericAssistDataElement_t; } GANSSGenericAssistDataElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSGenericAssistDataElement; extern asn_TYPE_descriptor_t asn_DEF_GANSSGenericAssistDataElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSSIonoStormFlags.h
View File

@ -15,24 +15,25 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSIonoStormFlags */ /* GANSSIonoStormFlags */
typedef struct GANSSIonoStormFlags typedef struct GANSSIonoStormFlags
{ {
long ionoStormFlag1; long ionoStormFlag1;
long ionoStormFlag2; long ionoStormFlag2;
long ionoStormFlag3; long ionoStormFlag3;
long ionoStormFlag4; long ionoStormFlag4;
long ionoStormFlag5; long ionoStormFlag5;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSIonoStormFlags_t; } GANSSIonoStormFlags_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSIonoStormFlags; extern asn_TYPE_descriptor_t asn_DEF_GANSSIonoStormFlags;
#ifdef __cplusplus #ifdef __cplusplus
} }

25
src/core/libs/supl/asn-rrlp/GANSSIonosphereModel.h
View File

@ -15,22 +15,23 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSIonosphereModel */ /* GANSSIonosphereModel */
typedef struct GANSSIonosphereModel typedef struct GANSSIonosphereModel
{ {
long ai0; long ai0;
long ai1; long ai1;
long ai2; long ai2;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSIonosphereModel_t; } GANSSIonosphereModel_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSIonosphereModel; extern asn_TYPE_descriptor_t asn_DEF_GANSSIonosphereModel;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSSIonosphericModel.h
View File

@ -15,28 +15,29 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct GANSSIonoStormFlags; struct GANSSIonoStormFlags;
/* GANSSIonosphericModel */ /* GANSSIonosphericModel */
typedef struct GANSSIonosphericModel typedef struct GANSSIonosphericModel
{ {
GANSSIonosphereModel_t ganssIonoModel; GANSSIonosphereModel_t ganssIonoModel;
struct GANSSIonoStormFlags *ganssIonoStormFlags /* OPTIONAL */; struct GANSSIonoStormFlags *ganssIonoStormFlags /* OPTIONAL */;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSIonosphericModel_t; } GANSSIonosphericModel_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSIonosphericModel; extern asn_TYPE_descriptor_t asn_DEF_GANSSIonosphericModel;
#ifdef __cplusplus #ifdef __cplusplus
} }

43
src/core/libs/supl/asn-rrlp/GANSSLocationInfo.h
View File

@ -20,35 +20,36 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct ReferenceFrame; struct ReferenceFrame;
/* GANSSLocationInfo */ /* GANSSLocationInfo */
typedef struct GANSSLocationInfo typedef struct GANSSLocationInfo
{ {
struct ReferenceFrame *referenceFrame /* OPTIONAL */; struct ReferenceFrame *referenceFrame /* OPTIONAL */;
GANSSTODm_t *ganssTODm /* OPTIONAL */; GANSSTODm_t *ganssTODm /* OPTIONAL */;
long *ganssTODFrac /* OPTIONAL */; long *ganssTODFrac /* OPTIONAL */;
GANSSTODUncertainty_t *ganssTODUncertainty /* OPTIONAL */; GANSSTODUncertainty_t *ganssTODUncertainty /* OPTIONAL */;
long *ganssTimeID /* OPTIONAL */; long *ganssTimeID /* OPTIONAL */;
FixType_t fixType; FixType_t fixType;
PositionData_t posData; PositionData_t posData;
long *stationaryIndication /* OPTIONAL */; long *stationaryIndication /* OPTIONAL */;
Ext_GeographicalInformation_t posEstimate; Ext_GeographicalInformation_t posEstimate;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSLocationInfo_t; } GANSSLocationInfo_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSLocationInfo; extern asn_TYPE_descriptor_t asn_DEF_GANSSLocationInfo;
#ifdef __cplusplus #ifdef __cplusplus
} }

21
src/core/libs/supl/asn-rrlp/GANSSMeasureInfo.h
View File

@ -15,20 +15,21 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSMeasureInfo */ /* GANSSMeasureInfo */
typedef struct GANSSMeasureInfo typedef struct GANSSMeasureInfo
{ {
SeqOfGANSS_MsrSetElement_t ganssMsrSetList; SeqOfGANSS_MsrSetElement_t ganssMsrSetList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSMeasureInfo_t; } GANSSMeasureInfo_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSMeasureInfo; extern asn_TYPE_descriptor_t asn_DEF_GANSSMeasureInfo;
#ifdef __cplusplus #ifdef __cplusplus
} }

29
src/core/libs/supl/asn-rrlp/GANSSNavModel.h
View File

@ -16,24 +16,25 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSNavModel */ /* GANSSNavModel */
typedef struct GANSSNavModel typedef struct GANSSNavModel
{ {
long nonBroadcastIndFlag; long nonBroadcastIndFlag;
long *toeMSB /* OPTIONAL */; long *toeMSB /* OPTIONAL */;
long *eMSB /* OPTIONAL */; long *eMSB /* OPTIONAL */;
long *sqrtAMBS /* OPTIONAL */; long *sqrtAMBS /* OPTIONAL */;
SeqOfGANSSSatelliteElement_t ganssSatelliteList; SeqOfGANSSSatelliteElement_t ganssSatelliteList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSNavModel_t; } GANSSNavModel_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSNavModel; extern asn_TYPE_descriptor_t asn_DEF_GANSSNavModel;
#ifdef __cplusplus #ifdef __cplusplus
} }

46
src/core/libs/supl/asn-rrlp/GANSSOrbitModel.h
View File

@ -15,36 +15,38 @@
#include <constr_CHOICE.h> #include <constr_CHOICE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum GANSSOrbitModel_PR { typedef enum GANSSOrbitModel_PR
GANSSOrbitModel_PR_NOTHING, /* No components present */
GANSSOrbitModel_PR_keplerianSet,
/* Extensions may appear below */
} GANSSOrbitModel_PR;
/* GANSSOrbitModel */
typedef struct GANSSOrbitModel
{
GANSSOrbitModel_PR present;
union GANSSOrbitModel_u
{ {
NavModel_KeplerianSet_t keplerianSet; GANSSOrbitModel_PR_NOTHING, /* No components present */
/* GANSSOrbitModel_PR_keplerianSet,
/* Extensions may appear below */
} GANSSOrbitModel_PR;
/* GANSSOrbitModel */
typedef struct GANSSOrbitModel
{
GANSSOrbitModel_PR present;
union GANSSOrbitModel_u
{
NavModel_KeplerianSet_t keplerianSet;
/*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
} choice; } choice;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSOrbitModel_t; } GANSSOrbitModel_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSOrbitModel; extern asn_TYPE_descriptor_t asn_DEF_GANSSOrbitModel;
#ifdef __cplusplus #ifdef __cplusplus
} }

40
src/core/libs/supl/asn-rrlp/GANSSPositioningMethod.h
View File

@ -14,29 +14,31 @@
#include <BIT_STRING.h> #include <BIT_STRING.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Dependencies */ /* Dependencies */
typedef enum GANSSPositioningMethod { typedef enum GANSSPositioningMethod
GANSSPositioningMethod_gps = 0, {
GANSSPositioningMethod_galileo = 1 GANSSPositioningMethod_gps = 0,
} e_GANSSPositioningMethod; GANSSPositioningMethod_galileo = 1
} e_GANSSPositioningMethod;
/* GANSSPositioningMethod */ /* GANSSPositioningMethod */
typedef BIT_STRING_t GANSSPositioningMethod_t; typedef BIT_STRING_t GANSSPositioningMethod_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSPositioningMethod; extern asn_TYPE_descriptor_t asn_DEF_GANSSPositioningMethod;
asn_struct_free_f GANSSPositioningMethod_free; asn_struct_free_f GANSSPositioningMethod_free;
asn_struct_print_f GANSSPositioningMethod_print; asn_struct_print_f GANSSPositioningMethod_print;
asn_constr_check_f GANSSPositioningMethod_constraint; asn_constr_check_f GANSSPositioningMethod_constraint;
ber_type_decoder_f GANSSPositioningMethod_decode_ber; ber_type_decoder_f GANSSPositioningMethod_decode_ber;
der_type_encoder_f GANSSPositioningMethod_encode_der; der_type_encoder_f GANSSPositioningMethod_encode_der;
xer_type_decoder_f GANSSPositioningMethod_decode_xer; xer_type_decoder_f GANSSPositioningMethod_decode_xer;
xer_type_encoder_f GANSSPositioningMethod_encode_xer; xer_type_encoder_f GANSSPositioningMethod_encode_xer;
per_type_decoder_f GANSSPositioningMethod_decode_uper; per_type_decoder_f GANSSPositioningMethod_decode_uper;
per_type_encoder_f GANSSPositioningMethod_encode_uper; per_type_encoder_f GANSSPositioningMethod_encode_uper;
#ifdef __cplusplus #ifdef __cplusplus
} }

21
src/core/libs/supl/asn-rrlp/GANSSRealTimeIntegrity.h
View File

@ -15,20 +15,21 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSRealTimeIntegrity */ /* GANSSRealTimeIntegrity */
typedef struct GANSSRealTimeIntegrity typedef struct GANSSRealTimeIntegrity
{ {
SeqOfBadSignalElement_t ganssBadSignalList; SeqOfBadSignalElement_t ganssBadSignalList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSRealTimeIntegrity_t; } GANSSRealTimeIntegrity_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSRealTimeIntegrity; extern asn_TYPE_descriptor_t asn_DEF_GANSSRealTimeIntegrity;
#ifdef __cplusplus #ifdef __cplusplus
} }

21
src/core/libs/supl/asn-rrlp/GANSSRefLocation.h
View File

@ -15,20 +15,21 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSRefLocation */ /* GANSSRefLocation */
typedef struct GANSSRefLocation typedef struct GANSSRefLocation
{ {
Ext_GeographicalInformation_t threeDLocation; Ext_GeographicalInformation_t threeDLocation;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSRefLocation_t; } GANSSRefLocation_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSRefLocation; extern asn_TYPE_descriptor_t asn_DEF_GANSSRefLocation;
#ifdef __cplusplus #ifdef __cplusplus
} }

23
src/core/libs/supl/asn-rrlp/GANSSRefMeasurementAssist.h
View File

@ -16,21 +16,22 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSRefMeasurementAssist */ /* GANSSRefMeasurementAssist */
typedef struct GANSSRefMeasurementAssist typedef struct GANSSRefMeasurementAssist
{ {
long *ganssSignalID /* OPTIONAL */; long *ganssSignalID /* OPTIONAL */;
SeqOfGANSSRefMeasurementElement_t ganssRefMeasAssitList; SeqOfGANSSRefMeasurementElement_t ganssRefMeasAssitList;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSRefMeasurementAssist_t; } GANSSRefMeasurementAssist_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSRefMeasurementAssist; extern asn_TYPE_descriptor_t asn_DEF_GANSSRefMeasurementAssist;
#ifdef __cplusplus #ifdef __cplusplus
} }

41
src/core/libs/supl/asn-rrlp/GANSSRefMeasurementElement.h
View File

@ -16,34 +16,35 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct AdditionalDopplerFields; struct AdditionalDopplerFields;
struct AddionalAngleFields; struct AddionalAngleFields;
/* GANSSRefMeasurementElement */ /* GANSSRefMeasurementElement */
typedef struct GANSSRefMeasurementElement typedef struct GANSSRefMeasurementElement
{ {
SVID_t svID; SVID_t svID;
long doppler0; long doppler0;
struct AdditionalDopplerFields *additionalDoppler /* OPTIONAL */; struct AdditionalDopplerFields *additionalDoppler /* OPTIONAL */;
long codePhase; long codePhase;
long intCodePhase; long intCodePhase;
long codePhaseSearchWindow; long codePhaseSearchWindow;
struct AddionalAngleFields *additionalAngle /* OPTIONAL */; struct AddionalAngleFields *additionalAngle /* OPTIONAL */;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSRefMeasurementElement_t; } GANSSRefMeasurementElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSRefMeasurementElement; extern asn_TYPE_descriptor_t asn_DEF_GANSSRefMeasurementElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

27
src/core/libs/supl/asn-rrlp/GANSSRefTimeInfo.h
View File

@ -17,23 +17,24 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSRefTimeInfo */ /* GANSSRefTimeInfo */
typedef struct GANSSRefTimeInfo typedef struct GANSSRefTimeInfo
{ {
long *ganssDay /* OPTIONAL */; long *ganssDay /* OPTIONAL */;
GANSSTOD_t ganssTOD; GANSSTOD_t ganssTOD;
GANSSTODUncertainty_t *ganssTODUncertainty /* OPTIONAL */; GANSSTODUncertainty_t *ganssTODUncertainty /* OPTIONAL */;
long *ganssTimeID /* OPTIONAL */; long *ganssTimeID /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSRefTimeInfo_t; } GANSSRefTimeInfo_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSRefTimeInfo; extern asn_TYPE_descriptor_t asn_DEF_GANSSRefTimeInfo;
#ifdef __cplusplus #ifdef __cplusplus
} }

27
src/core/libs/supl/asn-rrlp/GANSSReferenceTime.h
View File

@ -15,24 +15,25 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* Forward declarations */ /* Forward declarations */
struct GANSSTOD_GSMTimeAssociation; struct GANSSTOD_GSMTimeAssociation;
/* GANSSReferenceTime */ /* GANSSReferenceTime */
typedef struct GANSSReferenceTime typedef struct GANSSReferenceTime
{ {
GANSSRefTimeInfo_t ganssRefTimeInfo; GANSSRefTimeInfo_t ganssRefTimeInfo;
struct GANSSTOD_GSMTimeAssociation *ganssTOD_GSMTimeAssociation /* OPTIONAL */; struct GANSSTOD_GSMTimeAssociation *ganssTOD_GSMTimeAssociation /* OPTIONAL */;
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSReferenceTime_t; } GANSSReferenceTime_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSReferenceTime; extern asn_TYPE_descriptor_t asn_DEF_GANSSReferenceTime;
#ifdef __cplusplus #ifdef __cplusplus
} }

31
src/core/libs/supl/asn-rrlp/GANSSSatelliteElement.h
View File

@ -18,28 +18,29 @@
#include <constr_SEQUENCE.h> #include <constr_SEQUENCE.h>
#ifdef __cplusplus #ifdef __cplusplus
extern "C" { extern "C"
{
#endif #endif
/* GANSSSatelliteElement */ /* GANSSSatelliteElement */
typedef struct GANSSSatelliteElement typedef struct GANSSSatelliteElement
{ {
SVID_t svID; SVID_t svID;
long svHealth; long svHealth;
long iod; long iod;
GANSSClockModel_t ganssClockModel; GANSSClockModel_t ganssClockModel;
GANSSOrbitModel_t ganssOrbitModel; GANSSOrbitModel_t ganssOrbitModel;
/* /*
* This type is extensible, * This type is extensible,
* possible extensions are below. * possible extensions are below.
*/ */
/* Context for parsing across buffer boundaries */ /* Context for parsing across buffer boundaries */
asn_struct_ctx_t _asn_ctx; asn_struct_ctx_t _asn_ctx;
} GANSSSatelliteElement_t; } GANSSSatelliteElement_t;
/* Implementation */ /* Implementation */
extern asn_TYPE_descriptor_t asn_DEF_GANSSSatelliteElement; extern asn_TYPE_descriptor_t asn_DEF_GANSSSatelliteElement;
#ifdef __cplusplus #ifdef __cplusplus
} }

Some files were not shown because too many files have changed in this diff Show More