Making v2 tests CI ready

Change-Id: Ia32c9b2a1b5f833d1c7b078b678895b736d1e2a1

tests/featuretests/profiler/apps/vector_add_hip.cpp

@@ -0,0 +1,130 @@
+/*
+Copyright (c) 2015-2016 Advanced Micro Devices, Inc. All rights reserved.
+
+Permission is hereby granted, free of charge, to any person obtaining a copy
+of this software and associated documentation files (the "Software"), to deal
+in the Software without restriction, including without limitation the rights
+to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
+copies of the Software, and to permit persons to whom the Software is
+furnished to do so, subject to the following conditions:
+
+The above copyright notice and this permission notice shall be included in
+all copies or substantial portions of the Software.
+
+THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
+IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
+FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL THE
+AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
+LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
+OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
+THE SOFTWARE.
+*/
+#include <assert.h>
+#include <stdio.h>
+#include <stdlib.h>
+
+#include <algorithm>
+#include <iostream>
+
+#include "hip/hip_runtime.h"
+
+#define HIP_ASSERT(x) (assert((x) == hipSuccess))
+
+#define WIDTH 1024
+#define HEIGHT 1024
+
+#define NUM (WIDTH * HEIGHT)
+
+#define THREADS_PER_BLOCK_X 16
+#define THREADS_PER_BLOCK_Y 16
+#define THREADS_PER_BLOCK_Z 1
+
+__global__ void vectoradd_float(float *__restrict__ a,
+                                const float *__restrict__ b,
+                                const float *__restrict__ c, int width,
+                                int height) {
+  int x = hipBlockDim_x * hipBlockIdx_x + hipThreadIdx_x;
+  int y = hipBlockDim_y * hipBlockIdx_y + hipThreadIdx_y;
+
+  int i = y * width + x;
+  if (i < (width * height)) {
+    a[i] = b[i] + c[i];
+  }
+}
+
+int main() {
+  float *hostA;
+  float *hostB;
+  float *hostC;
+
+  float *deviceA;
+  float *deviceB;
+  float *deviceC;
+
+  hipDeviceProp_t devProp;
+  hipGetDeviceProperties(&devProp, 0);
+  std::cout << " System minor " << devProp.minor << std::endl;
+  std::cout << " System major " << devProp.major << std::endl;
+  std::cout << " agent prop name " << devProp.name << std::endl;
+
+  std::cout << "hip Device prop succeeded " << std::endl;
+
+  int i;
+  int errors;
+
+  hostA = reinterpret_cast<float *>(malloc(NUM * sizeof(float)));
+  hostB = reinterpret_cast<float *>(malloc(NUM * sizeof(float)));
+  hostC = reinterpret_cast<float *>(malloc(NUM * sizeof(float)));
+
+  // initialize the input data
+  for (i = 0; i < NUM; i++) {
+    hostB[i] = static_cast<float>(i);
+    hostC[i] = static_cast<float>(i) * 100.0f;
+  }
+
+  HIP_ASSERT(
+      hipMalloc(reinterpret_cast<void **>(&deviceA), NUM * sizeof(float)));
+  HIP_ASSERT(
+      hipMalloc(reinterpret_cast<void **>(&deviceB), NUM * sizeof(float)));
+  HIP_ASSERT(
+      hipMalloc(reinterpret_cast<void **>(&deviceC), NUM * sizeof(float)));
+
+  HIP_ASSERT(
+      hipMemcpy(deviceB, hostB, NUM * sizeof(float), hipMemcpyHostToDevice));
+  HIP_ASSERT(
+      hipMemcpy(deviceC, hostC, NUM * sizeof(float), hipMemcpyHostToDevice));
+
+  hipLaunchKernelGGL(
+      vectoradd_float,
+      dim3(WIDTH / THREADS_PER_BLOCK_X, HEIGHT / THREADS_PER_BLOCK_Y),
+      dim3(THREADS_PER_BLOCK_X, THREADS_PER_BLOCK_Y), 0, 0, deviceA, deviceB,
+      deviceC, WIDTH, HEIGHT);
+
+  HIP_ASSERT(
+      hipMemcpy(hostA, deviceA, NUM * sizeof(float), hipMemcpyDeviceToHost));
+
+  // verify the results
+  errors = 0;
+  for (i = 0; i < NUM; i++) {
+    if (hostA[i] != (hostB[i] + hostC[i])) {
+      errors++;
+    }
+  }
+  if (errors != 0) {
+    printf("FAILED: %d errors\n", errors);
+  } else {
+    printf("PASSED!\n");
+  }
+
+  HIP_ASSERT(hipFree(deviceA));
+  HIP_ASSERT(hipFree(deviceB));
+  HIP_ASSERT(hipFree(deviceC));
+
+  free(hostA);
+  free(hostB);
+  free(hostC);
+
+  // hipResetDefaultAccelerator();
+
+  return errors;
+}