onednn-src 0.1.13

/*******************************************************************************
* Copyright 2019 Intel Corporation
*
* Licensed under the Apache License, Version 2.0 (the "License");
* you may not use this file except in compliance with the License.
* You may obtain a copy of the License at
*
*     http://www.apache.org/licenses/LICENSE-2.0
*
* Unless required by applicable law or agreed to in writing, software
* distributed under the License is distributed on an "AS IS" BASIS,
* WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
* See the License for the specific language governing permissions and
* limitations under the License.
*******************************************************************************/

#ifndef CPU_SYCL_STREAM_CPU_THUNK_HPP
#define CPU_SYCL_STREAM_CPU_THUNK_HPP

#include "common/c_types_map.hpp"
#include "common/primitive_exec_types.hpp"

#include <stddef.h>
#include <stdint.h>
#include <vector>

namespace dnnl {
namespace impl {
namespace cpu {
namespace sycl {

struct submit_ctx_t {
    stream_t *stream = nullptr;
    const primitive_iface_t *prim_iface = nullptr;
    exec_ctx_t exec_ctx;
    std::vector<const memory_storage_t *> sycl_mem_storages;

    submit_ctx_t(const exec_ctx_t &exec_ctx) : exec_ctx(exec_ctx) {}
};

struct thunk_params_t {
    static constexpr size_t max_size = 32;

    size_t size;
    uintptr_t native_pointers[max_size];
    submit_ctx_t *submit_ctx_ptr;
};

} // namespace sycl
} // namespace cpu
} // namespace impl
} // namespace dnnl

void DNNL_API dnnl_impl_sycl_cpu_thunk(
        const dnnl::impl::cpu::sycl::thunk_params_t *params);

#endif // CPU_SYCL_STREAM_CPU_THUNK_HPP