90b320a6350b571861700b007d544aa1a34370ee
[o-du/phy.git] / fhi_lib / test / common / common.hpp
1 /******************************************************************************
2 *
3 *   Copyright (c) 2019 Intel.
4 *
5 *   Licensed under the Apache License, Version 2.0 (the "License");
6 *   you may not use this file except in compliance with the License.
7 *   You may obtain a copy of the License at
8 *
9 *       http://www.apache.org/licenses/LICENSE-2.0
10 *
11 *   Unless required by applicable law or agreed to in writing, software
12 *   distributed under the License is distributed on an "AS IS" BASIS,
13 *   WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
14 *   See the License for the specific language governing permissions and
15 *   limitations under the License.
16 *
17 *******************************************************************************/
18
19
20 /* This is the new utility file for all tests, all new common functionality has to go here.
21    When contributing to the common.hpp please focus on readability and maintainability rather than
22    execution time. */
23 #ifndef XRANLIB_COMMON_HPP
24 #define XRANLIB_COMMON_HPP
25
26 /* Disable warnings generated by JSON parser */
27 #pragma warning(disable : 191)
28 #pragma warning(disable : 186)
29 #pragma warning(disable : 192)
30
31 #include <exception>
32 #include <random>
33 #include <string>
34 #include <utility>
35 #include <vector>
36
37 #include <immintrin.h>
38 #include <malloc.h>
39
40 #define _BBLIB_DPDK_
41
42 #ifdef _BBLIB_DPDK_
43 #include <rte_config.h>
44 #include <rte_malloc.h>
45 #endif
46
47 #include "gtest/gtest.h"
48
49 #include "common_typedef_xran.h"
50
51 #include "json.hpp"
52
53 using json = nlohmann::json;
54
55 #define ASSERT_ARRAY_NEAR(reference, actual, size, precision) \
56         assert_array_near(reference, actual, size, precision)
57
58 #define ASSERT_ARRAY_EQ(reference, actual, size) \
59         assert_array_eq(reference, actual, size)
60
61 #define ASSERT_AVG_GREATER_COMPLEX(reference, actual, size, precision) \
62         assert_avg_greater_complex(reference, actual, size, precision)
63
64 struct BenchmarkParameters
65 {
66     static long repetition;
67     static long loop;
68     static unsigned cpu_id;
69 };
70
71 struct missing_config_file_exception : public std::exception
72 {
73     const char * what () const throw () override {
74         return "JSON file cannot be opened!";
75     }
76 };
77
78 struct reading_input_file_exception : public std::exception
79 {
80     const char * what () const throw () override {
81         return "Input file cannot be read!";
82     }
83 };
84
85 /*!
86     \brief Attach current process to the selected core.
87     \param [in] cpu Core number.
88     \return 0 on success, -1 otherwise.
89 */
90 int bind_to_cpu(const unsigned cpu);
91
92 /*!
93     \brief Calculate the mean and variance from the result of the run_benchmark.
94     \param [in] values Vector with result values.
95     \return std::pair where the first element is mean and the second one is standard deviation.
96     \note It's not a general mean/stddev function it only works properly when feed with data from
97           the benchmark function.
98 */
99 std::pair<double, double> calculate_statistics(const std::vector<long> values);
100
101 /*!
102     \brief For a given number return sequence of number from 0 to number - 1.
103     \param [in] number Positive integer value.
104     \return Vector with the sorted integer numbers between 0 and number - 1.
105 */
106 std::vector<unsigned> get_sequence(const unsigned number);
107
108 /*!
109     \brief Read JSON from the given file.
110     \param [in] filename name of the .json file.
111     \return JSON object with data.
112     \throws missing_config_file_exception when file cannot be opened.
113 */
114 json read_json_from_file(const std::string &filename);
115
116 /*!
117     \brief Read binary data from the file.
118     \param [in] filename name of the binary file.
119     \return Pointer to the allocated memory with data from the file.
120     \throws std::runtime_error when memory cannot be allocated.
121 */
122 char* read_data_to_aligned_array(const std::string &filename);
123
124 /*!
125     \brief Measure the TSC on the machine
126     \return Number of ticks per us
127 */
128 unsigned long tsc_recovery();
129
130 /*!
131     \brief Return the current value of the TSC
132     \return Current TSC value
133 */
134 unsigned long tsc_tick();
135
136 /*!
137     \class KernelTests
138
139     Each test class has to inherit from KernelTests class as it provides GTest support and does a lot
140     of setup (including JSON) an provides useful methods to operate on loaded JSON file.
141     Unfortunately GTest is limited in the way that all TEST_P within the class are called for all
142     cases/parameters, but we usually want two different data sets for functional and performance
143     tests (or maybe other types of tests). Because of that to use different data sets we need to
144     create separate classes, hence performance and functional test are in separate classes. it adds
145     an extra overhead, but adds much more flexibility. init_test(...) is used to select data set from
146     the JSON file.
147
148     Important note on the JSON file structure. Top JSON object can have as many section (JSON
149     objects) as needed, but each have to have a distinct name that is used by init_test. Then
150     each section must contain an array of objects (test cases) where each object has a name,
151     parameters and references. Everything inside parameters and references can be completely custom
152     as it's loaded by get_input/reference_parameter function. JSON values can be either literal
153     values, e.g. 1, 0.001, 5e-05, etc. or filename. Depends on the get type test framework can either
154     read the value or load data from the file - and it happens automatically (*pff* MAGIC!).
155 */
156 class KernelTests : public testing::TestWithParam<unsigned>
157 {
158 public:
159     static json conf;
160     static std::string test_type;
161
162     static void SetUpTestCase()
163     {
164         test_type = "None";
165
166         try
167         {
168             conf = read_json_from_file("conf.json");
169         }
170         catch(missing_config_file_exception &e)
171         {
172             std::cout << "[----------] SetUpTestCase failed: " << e.what() << std::endl;
173             exit(-1);
174         }
175
176         tsc = tsc_recovery();
177
178         if(!tsc)
179         {
180             std::cout << "[----------] SetUpTestCase failed: TSC recovery failed" << std::endl;
181             exit(-1);
182         }
183     }
184
185     static void TearDownTestCase()
186     {
187         /* Free resources - nothing to free at the moment */
188     }
189
190     static unsigned get_number_of_cases(const std::string &type)
191     {
192         try
193         {
194             json json_data = read_json_from_file("conf.json");
195
196             return json_data[type].size();
197         }
198         catch(missing_config_file_exception &e)
199         {
200             std::cout << "[----------] get_number_of_cases failed: " << e.what() << std::endl;
201
202             exit(-1);
203         }
204         catch(std::domain_error &e)
205         {
206             std::cout << "[----------] get_number_of_cases failed: " << e.what() << std::endl;
207             std::cout << "[----------] Use a default value: 0" << std::endl;
208
209             return 0;
210         }
211     }
212
213 protected:
214     double division_factor = 1.0;
215     std::string result_units = "None";
216     int parallelization_factor = 1;
217
218     /*!
219         \brief Set division factor
220         \param [in] factor Division factor that divides mean and standard deviation.
221     */
222     void set_division_factor(const double factor)
223     {
224         division_factor = factor;
225     }
226
227     /*!
228         \brief Set reults units
229         \param [in] units Units that are displayed in the report.
230     */
231     void set_results_units(const std::string &units)
232     {
233         result_units = units;
234     }
235
236     /*!
237         \brief Set size of processed data
238         \param [in] size Size of processed data used to calculate module throughput.
239     */
240     void set_parallelization_factor(const int factor)
241     {
242         parallelization_factor = factor;
243     }
244
245     /*!
246         \brief Run performance test case for a given function.
247         \param [in] isa Used Instruction Set.
248         \param [in] module_name name of the tested kernel.
249         \param [in] function function to be tested.
250         \param [in] args function's arguments.
251     */
252     template <typename F, typename ... Args>
253     void performance(const std::string &isa, const std::string &module_name, F function,
254                      Args ... args) {
255         ASSERT_EQ(0, bind_to_cpu(BenchmarkParameters::cpu_id)) << "Failed to bind to cpu!";
256
257         const auto result = run_benchmark(function, args ...);
258         const auto scaled_mean = result.first / division_factor / tsc;
259         const auto scaled_stddev = result.second / division_factor / tsc;
260
261         print_and_store_results(isa, get_case_name(), module_name, get_case_name(), result_units,
262                                 parallelization_factor, scaled_mean, scaled_stddev);
263     }
264
265     /*!
266         \brief Print unique test description to the results xml file
267         \param [in] isa Used Instruction Set.
268         \param [in] module_name name of the tested kernel.
269         \param [in] function function to be tested.
270     */
271     void print_test_description(const std::string &isa, const std::string &module_name) {
272         print_and_store_results(isa, get_case_name(), module_name, get_case_name(), result_units,
273                                 parallelization_factor, 0, 0);
274     }
275
276     //! @{
277     /*!
278         \brief Load selected data from a JSON object.
279          get_input_parameter loads data from parameters section of the test case in JSON file and
280          get_reference_parameter does the same thing for references section.
281
282          Get parameter function uses template type to figure out how to load parameters. If type
283          is NOT a pointer it'll load value directly from the JSON. Otherwise path to the test
284          vector is expected and function will allocate memory, load data from the binary file to
285          this memory location and return pointer to it. For example in here we request to load
286          pointer to float so llrs filed is expected to be
287          a path to the binary file.
288     */
289     template <typename T>
290     T get_input_parameter(const std::string &parameter_name)
291     {
292         try
293         {
294             return get_parameter<T>("parameters", parameter_name);
295         }
296         catch (std::domain_error &e)
297         {
298             std::cout << "[----------] get_input_parameter (" << parameter_name
299                       << ") failed: " << e.what()
300                       << ". Did you mispell the parameter name?" << std::endl;
301             throw;
302         }
303         catch(reading_input_file_exception &e)
304         {
305             std::cout << "[----------] get_input_parameter (" << parameter_name
306                       << ") failed: " << e.what() << std::endl;
307             throw;
308         }
309     }
310
311     template <typename T>
312     T get_reference_parameter(const std::string &parameter_name)
313     {
314         try
315         {
316             return get_parameter<T>("references", parameter_name);
317         }
318         catch (std::domain_error &e)
319         {
320             std::cout << "[----------] get_reference_parameter (" << parameter_name
321                       << ") failed: " << e.what()
322                       << ". Did you mispell the parameter name?" << std::endl;
323             throw;
324         }
325         catch(reading_input_file_exception &e)
326         {
327             std::cout << "[----------] get_reference_parameter (" << parameter_name
328                       << ") failed: " << e.what() << std::endl;
329             throw;
330         }
331     }
332     //! @}
333
334     /*!
335         \brief Get name of the test case from JSON file.
336         \return Test'ss case name or a default name if name field is missing.
337     */
338     const std::string get_case_name()
339     {
340         try
341         {
342             return conf[test_type][GetParam()]["name"];
343         }
344         catch (std::domain_error &e)
345         {
346             std::cout << "[----------] get_case_name failed: " << e.what()
347                       << ". Did you specify a test name in JSON?" << std::endl;
348             std::cout << "[----------] Using a default name instead" << std::endl;
349
350             return "Default test name";
351         }
352     }
353
354     /*!
355         \brief Defines section in the conf.json that is used to load parameters from.
356         \param [in] type Name of the section in the JSON file.
357     */
358     void init_test(const std::string &type)
359     {
360         test_type = type;
361         const std::string name = get_case_name();
362         std::cout << "[----------] Test case: " << name << std::endl;
363     }
364
365 private:
366     static unsigned long tsc;
367
368     template<typename T>
369     struct data_reader {
370         static T read_parameter(const int index, const std::string &type,
371                                 const std::string &parameter_name)
372         {
373             return conf[test_type][index][type][parameter_name];
374         }
375     };
376
377     template<typename T>
378     struct data_reader<std::vector<T>> {
379         static std::vector<T> read_parameter(const int index, const std::string &type,
380                                              const std::string &parameter_name)
381         {
382             auto array_size = conf[test_type][index][type][parameter_name].size();
383
384             std::vector<T> result(array_size);
385
386             for(unsigned number = 0; number < array_size; number++)
387                 result.at(number) = conf[test_type][index][type][parameter_name][number];
388
389             return result;
390         }
391     };
392
393     template<typename T>
394     struct data_reader<T*> {
395         static T* read_parameter(const int index, const std::string &type,
396                                  const std::string &parameter_name)
397         {
398             return (T*) read_data_to_aligned_array(conf[test_type][index][type][parameter_name]);
399         }
400     };
401
402     template <typename T>
403     T get_parameter(const std::string &type, const std::string &parameter_name)
404     {
405         return data_reader<T>::read_parameter(GetParam(), type, parameter_name);
406     }
407
408     void print_and_store_results(const std::string &isa,
409                                  const std::string &parameters,
410                                  const std::string &module_name,
411                                  const std::string &test_name,
412                                  const std::string &unit,
413                                  const int para_factor,
414                                  const double mean,
415                                  const double stddev);
416 };
417
418 /*!
419     \brief Run the given function and return the mean run time and stddev.
420     \param [in] function Function to benchmark.
421     \param [in] args Function's arguments.
422     \return std::pair where the first element is mean and the second one is standard deviation.
423 */
424 template <typename F, typename ... Args>
425 std::pair<double, double> run_benchmark(F function, Args ... args)
426 {
427     std::vector<long> results((unsigned long) BenchmarkParameters::repetition);
428
429     for(unsigned int outer_loop = 0; outer_loop < BenchmarkParameters::repetition; outer_loop++) {
430         const auto start_time =  __rdtsc();
431         for (unsigned int inner_loop = 0; inner_loop < BenchmarkParameters::loop; inner_loop++) {
432                 function(args ...);
433         }
434         const auto end_time = __rdtsc();
435         results.push_back(end_time - start_time);
436     }
437
438     return calculate_statistics(results);
439 };
440
441 /*!
442     \brief Assert elements of two arrays. It calls ASSERT_EQ for each element of the array.
443     \param [in] reference Array with reference values.
444     \param [in] actual Array with the actual output.
445     \param [in] size Size of the array.
446 */
447 template <typename T>
448 void assert_array_eq(const T* reference, const T* actual, const int size)
449 {
450     for(int index = 0; index < size ; index++)
451     {
452         ASSERT_EQ(reference[index], actual[index])
453                           <<"The wrong number is index: "<< index;
454     }
455 }
456
457 /*!
458     \brief Assert elements of two arrays. It calls ASSERT_NEAR for each element of the array.
459     \param [in] reference Array with reference values.
460     \param [in] actual Array with the actual output.
461     \param [in] size Size of the array.
462     \param [in] precision Precision fo the comparision used by ASSERT_NEAR.
463 */
464 template <typename T>
465 void assert_array_near(const T* reference, const T* actual, const int size, const double precision)
466 {
467     for(int index = 0; index < size ; index++)
468     {
469         ASSERT_NEAR(reference[index], actual[index], precision)
470                                 <<"The wrong number is index: "<< index;
471     }
472 }
473
474 template <>
475 void assert_array_near<complex_float>(const complex_float* reference, const complex_float* actual, const int size, const double precision)
476 {
477     for(int index = 0; index < size ; index++)
478     {
479         ASSERT_NEAR(reference[index].re, actual[index].re, precision)
480                              <<"The wrong number is RE, index: "<< index;
481         ASSERT_NEAR(reference[index].im, actual[index].im, precision)
482                              <<"The wrong number is IM, index: "<< index;
483     }
484 }
485
486 /*!
487     \brief Assert average diff of two arrays. It calls ASSERT_GT to check the average.
488     \param [in] reference Array with reference values, interleaved IQ inputs.
489     \param [in] actual Array with the actual output, interleaved IQ inputs.
490     \param [in] size Size of the array, based on complex inputs.
491     \param [in] precision Precision for the comparison used by ASSERT_GT.
492 */
493 template<typename T>
494 void assert_avg_greater_complex(const T* reference, const T* actual, const int size, const double precision)
495 {
496     float mseDB, MSE;
497     double avgMSEDB = 0.0;
498     for (int index = 0; index < size; index++) {
499         T refReal = reference[2*index];
500         T refImag = reference[(2*index)+1];
501         T resReal = actual[2*index];
502         T resImag = actual[(2*index)+1];
503
504         T errReal = resReal - refReal;
505         T errIm = resImag - refImag;
506
507         /* For some unit tests, e.g. PUCCH deomdulation, the expected output is 0. To avoid a
508            divide by zero error, check the reference results to determine if the expected result
509            is 0 and, if so, add a 1 to the division. */
510         if (refReal == 0 && refImag == 0)
511             MSE = (float)(errReal*errReal + errIm*errIm)/(float)(refReal*refReal + refImag*refImag + 1);
512         else
513             MSE = (float)(errReal*errReal + errIm*errIm)/(float)(refReal*refReal + refImag*refImag);
514
515         if(MSE == 0)
516             mseDB = (float)(-100.0);
517         else
518             mseDB = (float)(10.0) * (float)log10(MSE);
519
520         avgMSEDB += (double)mseDB;
521         }
522
523         avgMSEDB /= size;
524
525         ASSERT_GT(precision, avgMSEDB);
526 }
527
528 /*!
529     \brief Allocates memory of the given size.
530
531     aligned_malloc is wrapper to functions that allocate memory:
532     'rte_malloc' from DPDK if hugepages are defined, 'memalign' otherwise.
533     Size is defined as a number of variables of given type e.g. floats, rather than bytes.
534     It hides sizeof(T) multiplication and cast hence makes things cleaner.
535
536     \param [in] size Size of the memory to allocate.
537     \param [in] alignment Bytes alignment of the allocated memory. If 0, the return is a pointer
538                 that is suitably aligned for any kind of variable (in the same manner as malloc()).
539                 Otherwise, the return is a pointer that is a multiple of align. In this case,
540                 it must be a power of two. (Minimum alignment is the cacheline size, i.e. 64-bytes)
541     \return Pointer to the allocated memory.
542 */
543 template <typename T>
544 T* aligned_malloc(const int size, const unsigned alignment)
545 {
546 #ifdef _BBLIB_DPDK_
547     return (T*) rte_malloc(NULL, sizeof(T) * size, alignment);
548 #else
549 #ifndef _WIN64
550     return (T*) memalign(alignment, sizeof(T) * size);
551 #else
552     return (T*)_aligned_malloc(sizeof(T)*size, alignment);
553 #endif
554 #endif
555 }
556
557 /*!
558     \brief Frees memory pointed by the given pointer.
559
560     aligned_free is a wrapper for functions that free memory allocated by
561     aligned_malloc: 'rte_free' from DPDK if hugepages are defined and 'free' otherwise.
562
563     \param [in] ptr Pointer to the allocated memory.
564 */
565 template <typename T>
566 void aligned_free(T* ptr)
567 {
568 #ifdef _BBLIB_DPDK_
569     rte_free((void*)ptr);
570 #else
571
572 #ifndef _WIN64
573     free((void*)ptr);
574 #else
575     _aligned_free((void *)ptr);
576 #endif
577 #endif
578 }
579
580 /*!
581     \brief generate random numbers.
582
583     It allocates memory and populate it with random numbers using C++11 default engine and
584     uniform real / int distribution (where lo_range <= x <up_range). Don't forget to free
585     allocated memory!
586
587     \param [in] size Size of the memory to be filled with random data.
588     \param [in] alignment Bytes alignment of the memory.
589     \param [in] distribution Distribuiton for random generator.
590     \return Pointer to the allocated memory with random data.
591 */
592 template <typename T, typename U>
593 T* generate_random_numbers(const long size, const unsigned alignment, U& distribution)
594 {
595     auto array = (T*) aligned_malloc<char>(size * sizeof(T), alignment);
596
597     std::random_device random_device;
598     std::default_random_engine generator(random_device());
599
600     for(long i = 0; i < size; i++)
601         array[i] = (T)distribution(generator);
602
603     return array;
604 }
605
606 /*!
607     \brief generate random data.
608
609     It allocates memory and populate it with random data using C++11 default engine and
610     uniform integer distribution (bytes not floats are uniformly distributed). Don't forget
611     to free allocated memory!
612
613     \param [in] size Size of the memory to be filled with random data.
614     \param [in] alignment Bytes alignment of the memory.
615     \return Pointer to the allocated memory with random data.
616 */
617 template <typename T>
618 T* generate_random_data(const long size, const unsigned alignment)
619 {
620     std::uniform_int_distribution<> random(0, 255);
621
622     return (T*)generate_random_numbers<char, std::uniform_int_distribution<>>(size * sizeof(T), alignment, random);
623 }
624
625 /*!
626     \brief generate integer random numbers.
627
628     It allocates memory and populate it with random numbers using C++11 default engine and
629     uniform integer distribution (where lo_range <= x < up_range). Don't forget
630     to free allocated memory! The result type generated by the generator should be one of
631     int types.
632
633     \param [in] size Size of the memory to be filled with random data.
634     \param [in] alignment Bytes alignment of the memory.
635     \param [in] lo_range Lower bound of range of values returned by random generator.
636     \param [in] up_range Upper bound of range of values returned by random generator.
637     \return Pointer to the allocated memory with random data.
638 */
639 template <typename T>
640 T* generate_random_int_numbers(const long size, const unsigned alignment, const T lo_range,
641                                const T up_range)
642 {
643     std::uniform_int_distribution<T> random(lo_range, up_range);
644
645     return generate_random_numbers<T, std::uniform_int_distribution<T>>(size, alignment, random);
646 }
647
648 /*!
649     \brief generate real random numbers.
650
651     It allocates memory and populate it with random numbers using C++11 default engine and
652     uniform real distribution (where lo_range <= x <up_range). Don't forget to free
653     allocated memory! The result type generated by the generator should be one of
654     real types: float, double or long double.
655
656     \param [in] size Size of the memory to be filled with random data.
657     \param [in] alignment Bytes alignment of the memory.
658     \param [in] lo_range Lower bound of range of values returned by random generator.
659     \param [in] up_range Upper bound of range of values returned by random generator.
660     \return Pointer to the allocated memory with random data.
661 */
662 template <typename T>
663 T* generate_random_real_numbers(const long size, const unsigned alignment, const T lo_range,
664                                 const T up_range)
665 {
666     std::uniform_real_distribution<T> distribution(lo_range, up_range);
667
668     return generate_random_numbers<T, std::uniform_real_distribution<T>>(size, alignment, distribution);
669 }
670
671 #endif //XRANLIB_COMMON_HPP