#ifndef OPENMM_VECTORIZE_AVX2_H_
#define OPENMM_VECTORIZE_AVX2_H_

/* -------------------------------------------------------------------------- *
 *                                   OpenMM                                   *
 * -------------------------------------------------------------------------- *
 * This is part of the OpenMM molecular simulation toolkit.                   *
 * See https://openmm.org/development.                                        *
 *                                                                            *
 * Portions copyright (c) 2013-2014 Stanford University and the Authors.      *
 * Authors: Daniel Towner                                                     *
 * Contributors:                                                              *
 *                                                                            *
 * 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, CONTRIBUTORS 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 "vectorizeAvx.h"
#include <immintrin.h>

// This file defines classes and functions to simplify vectorizing code with AVX.

/** 
 * Derive from fvec8 so that default implementations of everything are provided,
 * but can be overriden with AVX2-specific variants where possible.
 */
class fvecAvx2 : public fvec8 {
public:

    fvecAvx2() = default;
    fvecAvx2(fvec8 v) : fvec8(v) {}
    fvecAvx2(float v) : fvec8(v) {}
    fvecAvx2(float v1, float v2, float v3, float v4, float v5, float v6, float v7, float v8) : fvec8(v8, v7, v6, v5, v4, v3, v2, v1) {}
    fvecAvx2(__m256 v) : fvec8(v) {}
    fvecAvx2(const float* v) : fvec8(v) {}

    /** Create a vector by gathering individual indexes of data from a table. Element i of the vector will
     * be loaded from table[idx[i]].
     * @param table The table from which to do a lookup.
     * @param indexes The indexes to gather.
     */
    fvecAvx2(const float* table, const int idx[8])
        : fvec8(_mm256_i32gather_ps(table, _mm256_loadu_si256((const __m256i*)idx), 4)) {}

    static fvecAvx2 expandBitsToMask(int bitmask);
};

inline fvecAvx2 fvecAvx2::expandBitsToMask(int bitmask) {
    // Put a copy of all bits into each vector element and then shift so that the
    // appropriate sub-bit becomes the MSB. For masking purposes, only the MSB matters and
    // the other bits can be completely arbitrary.
    const auto msb = _mm256_sllv_epi32(_mm256_set1_epi8(bitmask),
                                       _mm256_setr_epi32(7, 6, 5, 4, 3, 2, 1, 0));

    return _mm256_castsi256_ps(msb);
}

/**
 * Given a table of floating-point values and a set of indexes, perform a gather read into a pair
 * of vectors. The first result vector contains the values at the given indexes, and the second
 * result vector contains the values from each respective index+1.
 */
static inline void gatherVecPair(const float* table, ivec8 index, fvecAvx2& out0, fvecAvx2& out1) {
    const double* tableAsDbl = (const double*)table;

    // The input is a set of 8 indexes, each of which refers to a pair of floating point
    // values. The most efficient way to load from indexes in a vector is the gather instruction,
    // and the 64-bit variant should be used to get the pairs.

    // Given indexes ABCDEFGH, load the pairs corresponding to A C E G. This gives a set of
    // 4 pairs. The high indexes (in the upper part of each 64-bit index) are cleared.
    const auto lowerIdx = _mm256_and_si256(index, _mm256_set1_epi64x(0xFFFFFFFF));
    const auto lowerGather = _mm256_castpd_ps(_mm256_i64gather_pd(tableAsDbl, lowerIdx, 4));

    // Load indexes B D F H, this time by shifting the high 32-bit indexes into the lower 32-bits.
    const auto upperIdx = _mm256_srli_epi64(index, 32);
    const auto upperGather = _mm256_castpd_ps(_mm256_i64gather_pd(tableAsDbl, upperIdx, 4));

    // All the first values must now be brought together. The lower values are already in the
    // correct place, but the upper gather values must be moved over and blended in.
    const auto swapUpper = _mm256_permute_ps(upperGather, 0b10110001);
    out0 = fvecAvx2(_mm256_blend_ps(lowerGather, swapUpper, 0b10101010));

    // And the same for the upper values.
    const auto swapLower = _mm256_permute_ps(lowerGather, 0b10110001);
    out1 = fvecAvx2(_mm256_blend_ps(swapLower, upperGather, 0b10101010));

}

#endif /*OPENMM_VECTORIZE_AVX2_H_*/
