Skip if FMA available [skip ci]

Updated changelog [skip ci]
Fixed CI
2026-07-22 03:57:34 +08:00 · 2024-04-14 14:17:10 -07:00 · 2024-04-13 20:23:33 -07:00 · 2024-04-13 20:17:33 -07:00 · 2024-04-13 20:12:47 -07:00
36 changed files with 261 additions and 2336 deletions
--- a/.github/workflows/build.yml
+++ b/.github/workflows/build.yml
@@ -115,8 +115,6 @@ jobs:
          sudo -u postgres make prove_installcheck
        env:
          PG_CFLAGS: -DUSE_ASSERT_CHECKING -Wall -Wextra -Werror -Wno-unused-parameter -Wno-sign-compare
-      - if: ${{ failure() }}
-        run: cat pgvector/regression.diffs
  valgrind:
    if: ${{ !startsWith(github.ref_name, 'mac') && !startsWith(github.ref_name, 'windows') }}
    runs-on: ubuntu-latest
--- a/CHANGELOG.md
+++ b/CHANGELOG.md
@@ -3,12 +3,10 @@
 - Added `halfvec` type
 - Added `sparsevec` type
 - Added support for `bit` vectors to HNSW
- Added `binary_quantize` function
 - Added `hamming_distance` function
 - Added `jaccard_distance` function
- Added `l2_normalize` function
+- Added `quantize_binary` function
 - Added `subvector` function
- Added concatenate operator for vectors
 - Added CPU dispatching for distance functions on Linux x86-64
 - Updated comparison operators to support vectors with different dimensions

--- a/Makefile.win
+++ b/Makefile.win
@@ -4,7 +4,7 @@ EXTVERSION = 0.6.2
 OBJS = src\bitvector.obj src\halfutils.obj src\halfvec.obj src\hnsw.obj src\hnswbuild.obj src\hnswinsert.obj src\hnswscan.obj src\hnswutils.obj src\hnswvacuum.obj src\ivfbuild.obj src\ivfflat.obj src\ivfinsert.obj src\ivfkmeans.obj src\ivfscan.obj src\ivfutils.obj src\ivfvacuum.obj src\sparsevec.obj src\vector.obj
 HEADERS = src\halfvec.h src\sparsevec.h src\vector.h

-REGRESS = bit_functions btree_halfvec btree_sparsevec btree_vector cast copy halfvec_functions halfvec_input hnsw_bit_hamming hnsw_bit_jaccard hnsw_halfvec_cosine hnsw_halfvec_ip hnsw_halfvec_l2 hnsw_options hnsw_sparsevec_cosine hnsw_sparsevec_ip hnsw_sparsevec_l2 hnsw_unlogged hnsw_vector_cosine hnsw_vector_ip hnsw_vector_l2 ivfflat_halfvec_cosine ivfflat_halfvec_ip ivfflat_halfvec_l2 ivfflat_options ivfflat_unlogged ivfflat_vector_cosine ivfflat_vector_ip ivfflat_vector_l2 sparsevec_functions sparsevec_input vector_functions vector_input
+REGRESS = bit_functions btree cast copy halfvec_functions halfvec_input hnsw_bit_hamming hnsw_bit_jaccard hnsw_halfvec_cosine hnsw_halfvec_ip hnsw_halfvec_l2 hnsw_options hnsw_sparsevec_cosine hnsw_sparsevec_ip hnsw_sparsevec_l2 hnsw_unlogged hnsw_vector_cosine hnsw_vector_ip hnsw_vector_l2 ivfflat_options ivfflat_unlogged ivfflat_vector_cosine ivfflat_vector_ip ivfflat_vector_l2 sparsevec_functions sparsevec_input vector_functions vector_input
 REGRESS_OPTS = --inputdir=test --load-extension=$(EXTENSION)

 # For /arch flags
--- a/README.md
+++ b/README.md
@@ -138,12 +138,6 @@ Get the nearest neighbors to a vector
 SELECT * FROM items ORDER BY embedding <-> '[3,1,2]' LIMIT 5;
 ```

-Supported distance functions are:
-
- `<->` - L2 distance
- `<#>` - (negative) inner product
- `<=>` - cosine distance
-
 Get the nearest neighbors to a row

 ```sql
@@ -482,20 +476,20 @@ Also supports Jaccard distance (`<%>`)
 Use expression indexing for binary quantization

 ```sql
-CREATE INDEX ON items USING hnsw ((binary_quantize(embedding)::bit(3)) bit_hamming_ops);
+CREATE INDEX ON items USING hnsw ((quantize_binary(embedding)::bit(3)) bit_hamming_ops);
 ```

 Get the nearest neighbors by Hamming distance

 ```sql
-SELECT * FROM items ORDER BY binary_quantize(embedding)::bit(3) <~> binary_quantize('[1,-2,3]') LIMIT 5;
+SELECT * FROM items ORDER BY quantize_binary(embedding)::bit(3) <~> quantize_binary('[1,-2,3]') LIMIT 5;
 ```

 Re-rank by the original vectors for better recall

 ```sql
 SELECT * FROM (
-    SELECT * FROM items ORDER BY binary_quantize(embedding)::bit(3) <~> binary_quantize('[1,-2,3]') LIMIT 20
+    SELECT * FROM items ORDER BY quantize_binary(embedding)::bit(3) <~> quantize_binary('[1,-2,3]') LIMIT 20
 ) ORDER BY embedding <=> '[1,-2,3]' LIMIT 5;
 ```

@@ -515,7 +509,7 @@ Insert vectors
 INSERT INTO items (embedding) VALUES ('{1:1,3:2,5:3}/5'), ('{1:4,3:5,5:6}/5');
 ```

-The format is `{index1:value1,index2:value2}/dimensions` and indices start at 1 like SQL arrays
+Note: The format is `{index1:value1,index2:value2,...}/dimensions` and indices start at 1 like SQL arrays

 Get the nearest neighbors by L2 distance

@@ -850,7 +844,6 @@ Operator | Description | Added
 \+ | element-wise addition |
 \- | element-wise subtraction |
 \* | element-wise multiplication | 0.5.0
-\|\| | concatenate | unreleased
 <-> | Euclidean distance |
 <#> | negative inner product |
 <=> | cosine distance |
@@ -859,12 +852,11 @@ Operator | Description | Added

 Function | Description | Added
 --- | --- | ---
-binary_quantize(vector) → bit | binary quantize | unreleased
 cosine_distance(vector, vector) → double precision | cosine distance |
 inner_product(vector, vector) → double precision | inner product |
-l1_distance(vector, vector) → double precision | taxicab distance | 0.5.0
 l2_distance(vector, vector) → double precision | Euclidean distance |
-l2_normalize(vector) → vector | Normalize with Euclidean norm | unreleased
+l1_distance(vector, vector) → double precision | taxicab distance | 0.5.0
+quantize_binary(vector) → bit | quantize | unreleased
 subvector(vector, integer, integer) → vector | subvector | unreleased
 vector_dims(vector) → integer | number of dimensions |
 vector_norm(vector) → double precision | Euclidean norm |
@@ -884,10 +876,6 @@ Each half vector takes `2 * dimensions + 8` bytes of storage. Each element is a

 Operator | Description | Added
 --- | --- | ---
-\+ | element-wise addition | unreleased
-\- | element-wise subtraction | unreleased
-\* | element-wise multiplication | unreleased
-\|\| | concatenate | unreleased
 <-> | Euclidean distance | unreleased
 <#> | negative inner product | unreleased
 <=> | cosine distance | unreleased
@@ -896,22 +884,12 @@ Operator | Description | Added

 Function | Description | Added
 --- | --- | ---
-binary_quantize(halfvec) → bit | binary quantize | unreleased
 cosine_distance(halfvec, halfvec) → double precision | cosine distance | unreleased
 inner_product(halfvec, halfvec) → double precision | inner product | unreleased
-l1_distance(halfvec, halfvec) → double precision | taxicab distance | unreleased
 l2_distance(halfvec, halfvec) → double precision | Euclidean distance | unreleased
-l2_norm(halfvec) → double precision | Euclidean norm | unreleased
-l2_normalize(halfvec) → halfvec | Normalize with Euclidean norm | unreleased
+l1_distance(halfvec, halfvec) → double precision | taxicab distance | unreleased
+quantize_binary(halfvec) → bit | quantize | unreleased
 subvector(halfvec, integer, integer) → halfvec | subvector | unreleased
-vector_dims(halfvec) → integer | number of dimensions | unreleased
-
-### Halfvec Aggregate Functions
-
-Function | Description | Added
--- | --- | ---
-avg(halfvec) → halfvec | average | unreleased
-sum(halfvec) → halfvec | sum | unreleased

 ### Bit Type

@@ -949,10 +927,8 @@ Function | Description | Added
 --- | --- | ---
 cosine_distance(sparsevec, sparsevec) → double precision | cosine distance | unreleased
 inner_product(sparsevec, sparsevec) → double precision | inner product | unreleased
-l1_distance(sparsevec, sparsevec) → double precision | taxicab distance | unreleased
 l2_distance(sparsevec, sparsevec) → double precision | Euclidean distance | unreleased
-l2_norm(sparsevec) → double precision | Euclidean norm | unreleased
-l2_normalize(sparsevec) → sparsevec | Normalize with Euclidean norm | unreleased
+l1_distance(sparsevec, sparsevec) → double precision | taxicab distance | unreleased

 ## Installation Notes - Linux and Mac

@@ -1079,7 +1055,7 @@ Note: Replace `16` with your Postgres server version
 Install the FreeBSD package with:

 ```sh
-pkg install postgresql15-pgvector
+pkg install postgresql15-pg_vector
 ```

 or the port with:
--- a/sql/vector--0.6.2--0.7.0.sql
+++ b/sql/vector--0.6.2--0.7.0.sql
@@ -1,22 +1,12 @@
 -- complain if script is sourced in psql, rather than via CREATE EXTENSION
 \echo Use "ALTER EXTENSION vector UPDATE TO '0.7.0'" to load this file. \quit

-CREATE FUNCTION l2_normalize(vector) RETURNS vector
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION binary_quantize(vector) RETURNS bit
+CREATE FUNCTION quantize_binary(vector) RETURNS bit
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

 CREATE FUNCTION subvector(vector, int, int) RETURNS vector
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION vector_concat(vector, vector) RETURNS vector
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE OPERATOR || (
-	LEFTARG = vector, RIGHTARG = vector, PROCEDURE = vector_concat
-);
-
 CREATE FUNCTION hamming_distance(bit, bit) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -81,54 +71,15 @@ CREATE FUNCTION cosine_distance(halfvec, halfvec) RETURNS float8
 CREATE FUNCTION l1_distance(halfvec, halfvec) RETURNS float8
 	AS 'MODULE_PATHNAME', 'halfvec_l1_distance' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION vector_dims(halfvec) RETURNS integer
-	AS 'MODULE_PATHNAME', 'halfvec_vector_dims' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+CREATE FUNCTION halfvec_norm(halfvec) RETURNS float8
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION l2_norm(halfvec) RETURNS float8
-	AS 'MODULE_PATHNAME', 'halfvec_l2_norm' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION l2_normalize(halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME', 'halfvec_l2_normalize' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION binary_quantize(halfvec) RETURNS bit
-	AS 'MODULE_PATHNAME', 'halfvec_binary_quantize' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+CREATE FUNCTION quantize_binary(halfvec) RETURNS bit
+	AS 'MODULE_PATHNAME', 'halfvec_quantize_binary' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

 CREATE FUNCTION subvector(halfvec, int, int) RETURNS halfvec
 	AS 'MODULE_PATHNAME', 'halfvec_subvector' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION halfvec_add(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_sub(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_mul(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_concat(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_lt(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_le(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_eq(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_ne(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_ge(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_gt(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_cmp(halfvec, halfvec) RETURNS int4
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
 CREATE FUNCTION halfvec_l2_squared_distance(halfvec, halfvec) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -138,37 +89,9 @@ CREATE FUNCTION halfvec_negative_inner_product(halfvec, halfvec) RETURNS float8
 CREATE FUNCTION halfvec_spherical_distance(halfvec, halfvec) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION halfvec_accum(double precision[], halfvec) RETURNS double precision[]
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_avg(double precision[]) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE AGGREGATE avg(halfvec) (
-	SFUNC = halfvec_accum,
-	STYPE = double precision[],
-	FINALFUNC = halfvec_avg,
-	COMBINEFUNC = vector_combine,
-	INITCOND = '{0}',
-	PARALLEL = SAFE
-);
-
-CREATE AGGREGATE sum(halfvec) (
-	SFUNC = halfvec_add,
-	STYPE = halfvec,
-	COMBINEFUNC = halfvec_add,
-	PARALLEL = SAFE
-);
-
 CREATE FUNCTION halfvec(halfvec, integer, boolean) RETURNS halfvec
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION halfvec_to_vector(halfvec, integer, boolean) RETURNS vector
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION vector_to_halfvec(vector, integer, boolean) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
 CREATE FUNCTION array_to_halfvec(integer[], integer, boolean) RETURNS halfvec
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -187,14 +110,8 @@ CREATE FUNCTION halfvec_to_float4(halfvec, integer, boolean) RETURNS real[]
 CREATE CAST (halfvec AS halfvec)
 	WITH FUNCTION halfvec(halfvec, integer, boolean) AS IMPLICIT;

-CREATE CAST (halfvec AS vector)
-	WITH FUNCTION halfvec_to_vector(halfvec, integer, boolean) AS ASSIGNMENT;
-
-CREATE CAST (vector AS halfvec)
-	WITH FUNCTION vector_to_halfvec(vector, integer, boolean) AS IMPLICIT;
-
 CREATE CAST (halfvec AS real[])
-	WITH FUNCTION halfvec_to_float4(halfvec, integer, boolean) AS ASSIGNMENT;
+	WITH FUNCTION halfvec_to_float4(halfvec, integer, boolean) AS IMPLICIT;

 CREATE CAST (integer[] AS halfvec)
 	WITH FUNCTION array_to_halfvec(integer[], integer, boolean) AS ASSIGNMENT;
@@ -223,69 +140,6 @@ CREATE OPERATOR <=> (
 	COMMUTATOR = '<=>'
 );

-CREATE OPERATOR + (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_add,
-	COMMUTATOR = +
-);
-
-CREATE OPERATOR - (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_sub
-);
-
-CREATE OPERATOR * (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_mul,
-	COMMUTATOR = *
-);
-
-CREATE OPERATOR || (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_concat
-);
-
-CREATE OPERATOR < (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_lt,
-	COMMUTATOR = > , NEGATOR = >= ,
-	RESTRICT = scalarltsel, JOIN = scalarltjoinsel
-);
-
-CREATE OPERATOR <= (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_le,
-	COMMUTATOR = >= , NEGATOR = > ,
-	RESTRICT = scalarlesel, JOIN = scalarlejoinsel
-);
-
-CREATE OPERATOR = (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_eq,
-	COMMUTATOR = = , NEGATOR = <> ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR <> (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_ne,
-	COMMUTATOR = <> , NEGATOR = = ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR >= (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_ge,
-	COMMUTATOR = <= , NEGATOR = < ,
-	RESTRICT = scalargesel, JOIN = scalargejoinsel
-);
-
-CREATE OPERATOR > (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_gt,
-	COMMUTATOR = < , NEGATOR = <= ,
-	RESTRICT = scalargtsel, JOIN = scalargtjoinsel
-);
-
-CREATE OPERATOR CLASS halfvec_ops
-	DEFAULT FOR TYPE halfvec USING btree AS
-	OPERATOR 1 < ,
-	OPERATOR 2 <= ,
-	OPERATOR 3 = ,
-	OPERATOR 4 >= ,
-	OPERATOR 5 > ,
-	FUNCTION 1 halfvec_cmp(halfvec, halfvec);
-
 CREATE OPERATOR CLASS halfvec_l2_ops
 	FOR TYPE halfvec USING ivfflat AS
 	OPERATOR 1 <-> (halfvec, halfvec) FOR ORDER BY float_ops,
@@ -297,15 +151,15 @@ CREATE OPERATOR CLASS halfvec_ip_ops
 	OPERATOR 1 <#> (halfvec, halfvec) FOR ORDER BY float_ops,
 	FUNCTION 1 halfvec_negative_inner_product(halfvec, halfvec),
 	FUNCTION 3 halfvec_spherical_distance(halfvec, halfvec),
-	FUNCTION 4 l2_norm(halfvec);
+	FUNCTION 4 halfvec_norm(halfvec);

 CREATE OPERATOR CLASS halfvec_cosine_ops
 	FOR TYPE halfvec USING ivfflat AS
 	OPERATOR 1 <=> (halfvec, halfvec) FOR ORDER BY float_ops,
 	FUNCTION 1 halfvec_negative_inner_product(halfvec, halfvec),
-	FUNCTION 2 l2_norm(halfvec),
+	FUNCTION 2 halfvec_norm(halfvec),
 	FUNCTION 3 halfvec_spherical_distance(halfvec, halfvec),
-	FUNCTION 4 l2_norm(halfvec);
+	FUNCTION 4 halfvec_norm(halfvec);

 CREATE OPERATOR CLASS halfvec_l2_ops
 	FOR TYPE halfvec USING hnsw AS
@@ -321,7 +175,19 @@ CREATE OPERATOR CLASS halfvec_cosine_ops
 	FOR TYPE halfvec USING hnsw AS
 	OPERATOR 1 <=> (halfvec, halfvec) FOR ORDER BY float_ops,
 	FUNCTION 1 halfvec_negative_inner_product(halfvec, halfvec),
-	FUNCTION 2 l2_norm(halfvec);
+	FUNCTION 2 halfvec_norm(halfvec);
+
+CREATE FUNCTION halfvec_to_vector(halfvec, integer, boolean) RETURNS vector
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+
+CREATE FUNCTION vector_to_halfvec(vector, integer, boolean) RETURNS halfvec
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+
+CREATE CAST (halfvec AS vector)
+	WITH FUNCTION halfvec_to_vector(halfvec, integer, boolean) AS IMPLICIT;
+
+CREATE CAST (vector AS halfvec)
+	WITH FUNCTION vector_to_halfvec(vector, integer, boolean) AS IMPLICIT;

 CREATE TYPE sparsevec;

@@ -358,34 +224,7 @@ CREATE FUNCTION inner_product(sparsevec, sparsevec) RETURNS float8
 CREATE FUNCTION cosine_distance(sparsevec, sparsevec) RETURNS float8
 	AS 'MODULE_PATHNAME', 'sparsevec_cosine_distance' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION l1_distance(sparsevec, sparsevec) RETURNS float8
-	AS 'MODULE_PATHNAME', 'sparsevec_l1_distance' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION l2_norm(sparsevec) RETURNS float8
-	AS 'MODULE_PATHNAME', 'sparsevec_l2_norm' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION l2_normalize(sparsevec) RETURNS sparsevec
-	AS 'MODULE_PATHNAME', 'sparsevec_l2_normalize' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_lt(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_le(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_eq(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_ne(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_ge(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_gt(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_cmp(sparsevec, sparsevec) RETURNS int4
+CREATE FUNCTION sparsevec_norm(sparsevec) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

 CREATE FUNCTION sparsevec_l2_squared_distance(sparsevec, sparsevec) RETURNS float8
@@ -407,7 +246,7 @@ CREATE CAST (sparsevec AS sparsevec)
 	WITH FUNCTION sparsevec(sparsevec, integer, boolean) AS IMPLICIT;

 CREATE CAST (sparsevec AS vector)
-	WITH FUNCTION sparsevec_to_vector(sparsevec, integer, boolean) AS ASSIGNMENT;
+	WITH FUNCTION sparsevec_to_vector(sparsevec, integer, boolean) AS IMPLICIT;

 CREATE CAST (vector AS sparsevec)
 	WITH FUNCTION vector_to_sparsevec(vector, integer, boolean) AS IMPLICIT;
@@ -427,51 +266,6 @@ CREATE OPERATOR <=> (
 	COMMUTATOR = '<=>'
 );

-CREATE OPERATOR < (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_lt,
-	COMMUTATOR = > , NEGATOR = >= ,
-	RESTRICT = scalarltsel, JOIN = scalarltjoinsel
-);
-
-CREATE OPERATOR <= (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_le,
-	COMMUTATOR = >= , NEGATOR = > ,
-	RESTRICT = scalarlesel, JOIN = scalarlejoinsel
-);
-
-CREATE OPERATOR = (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_eq,
-	COMMUTATOR = = , NEGATOR = <> ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR <> (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_ne,
-	COMMUTATOR = <> , NEGATOR = = ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR >= (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_ge,
-	COMMUTATOR = <= , NEGATOR = < ,
-	RESTRICT = scalargesel, JOIN = scalargejoinsel
-);
-
-CREATE OPERATOR > (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_gt,
-	COMMUTATOR = < , NEGATOR = <= ,
-	RESTRICT = scalargtsel, JOIN = scalargtjoinsel
-);
-
-CREATE OPERATOR CLASS sparsevec_ops
-	DEFAULT FOR TYPE sparsevec USING btree AS
-	OPERATOR 1 < ,
-	OPERATOR 2 <= ,
-	OPERATOR 3 = ,
-	OPERATOR 4 >= ,
-	OPERATOR 5 > ,
-	FUNCTION 1 sparsevec_cmp(sparsevec, sparsevec);
-
 CREATE OPERATOR CLASS sparsevec_l2_ops
 	FOR TYPE sparsevec USING hnsw AS
 	OPERATOR 1 <-> (sparsevec, sparsevec) FOR ORDER BY float_ops,
@@ -486,4 +280,4 @@ CREATE OPERATOR CLASS sparsevec_cosine_ops
 	FOR TYPE sparsevec USING hnsw AS
 	OPERATOR 1 <=> (sparsevec, sparsevec) FOR ORDER BY float_ops,
 	FUNCTION 1 sparsevec_negative_inner_product(sparsevec, sparsevec),
-	FUNCTION 2 l2_norm(sparsevec);
+	FUNCTION 2 sparsevec_norm(sparsevec);
--- a/sql/vector.sql
+++ b/sql/vector.sql
@@ -26,9 +26,7 @@ CREATE TYPE vector (
 	TYPMOD_IN = vector_typmod_in,
 	RECEIVE   = vector_recv,
 	SEND      = vector_send,
-	STORAGE   = external,
-	CATEGORY  = 'v',
-	PREFERRED = true
+	STORAGE   = external
 );

 -- vector functions
@@ -51,17 +49,6 @@ CREATE FUNCTION vector_dims(vector) RETURNS integer
 CREATE FUNCTION vector_norm(vector) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION l2_normalize(vector) RETURNS vector
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION binary_quantize(vector) RETURNS bit
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION subvector(vector, int, int) RETURNS vector
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-- vector private functions
-
 CREATE FUNCTION vector_add(vector, vector) RETURNS vector
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -71,9 +58,14 @@ CREATE FUNCTION vector_sub(vector, vector) RETURNS vector
 CREATE FUNCTION vector_mul(vector, vector) RETURNS vector
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION vector_concat(vector, vector) RETURNS vector
+CREATE FUNCTION quantize_binary(vector) RETURNS bit
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

+CREATE FUNCTION subvector(vector, int, int) RETURNS vector
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+
+-- vector private functions
+
 CREATE FUNCTION vector_lt(vector, vector) RETURNS bool
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -202,10 +194,6 @@ CREATE OPERATOR * (
 	COMMUTATOR = *
 );

-CREATE OPERATOR || (
-	LEFTARG = vector, RIGHTARG = vector, PROCEDURE = vector_concat
-);
-
 CREATE OPERATOR < (
 	LEFTARG = vector, RIGHTARG = vector, PROCEDURE = vector_lt,
 	COMMUTATOR = > , NEGATOR = >= ,
@@ -359,8 +347,7 @@ CREATE TYPE halfvec (
 	TYPMOD_IN = halfvec_typmod_in,
 	RECEIVE   = halfvec_recv,
 	SEND      = halfvec_send,
-	STORAGE   = external,
-	CATEGORY  = 'v'
+	STORAGE   = external
 );

 -- halfvec functions
@@ -377,56 +364,17 @@ CREATE FUNCTION cosine_distance(halfvec, halfvec) RETURNS float8
 CREATE FUNCTION l1_distance(halfvec, halfvec) RETURNS float8
 	AS 'MODULE_PATHNAME', 'halfvec_l1_distance' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION vector_dims(halfvec) RETURNS integer
-	AS 'MODULE_PATHNAME', 'halfvec_vector_dims' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+CREATE FUNCTION halfvec_norm(halfvec) RETURNS float8
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION l2_norm(halfvec) RETURNS float8
-	AS 'MODULE_PATHNAME', 'halfvec_l2_norm' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION l2_normalize(halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME', 'halfvec_l2_normalize' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION binary_quantize(halfvec) RETURNS bit
-	AS 'MODULE_PATHNAME', 'halfvec_binary_quantize' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+CREATE FUNCTION quantize_binary(halfvec) RETURNS bit
+	AS 'MODULE_PATHNAME', 'halfvec_quantize_binary' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

 CREATE FUNCTION subvector(halfvec, int, int) RETURNS halfvec
 	AS 'MODULE_PATHNAME', 'halfvec_subvector' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

 -- halfvec private functions

-CREATE FUNCTION halfvec_add(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_sub(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_mul(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_concat(halfvec, halfvec) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_lt(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_le(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_eq(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_ne(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_ge(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_gt(halfvec, halfvec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_cmp(halfvec, halfvec) RETURNS int4
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
 CREATE FUNCTION halfvec_l2_squared_distance(halfvec, halfvec) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -436,41 +384,11 @@ CREATE FUNCTION halfvec_negative_inner_product(halfvec, halfvec) RETURNS float8
 CREATE FUNCTION halfvec_spherical_distance(halfvec, halfvec) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION halfvec_accum(double precision[], halfvec) RETURNS double precision[]
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION halfvec_avg(double precision[]) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-- halfvec aggregates
-
-CREATE AGGREGATE avg(halfvec) (
-	SFUNC = halfvec_accum,
-	STYPE = double precision[],
-	FINALFUNC = halfvec_avg,
-	COMBINEFUNC = vector_combine,
-	INITCOND = '{0}',
-	PARALLEL = SAFE
-);
-
-CREATE AGGREGATE sum(halfvec) (
-	SFUNC = halfvec_add,
-	STYPE = halfvec,
-	COMBINEFUNC = halfvec_add,
-	PARALLEL = SAFE
-);
-
 -- halfvec cast functions

 CREATE FUNCTION halfvec(halfvec, integer, boolean) RETURNS halfvec
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION halfvec_to_vector(halfvec, integer, boolean) RETURNS vector
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION vector_to_halfvec(vector, integer, boolean) RETURNS halfvec
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
 CREATE FUNCTION array_to_halfvec(integer[], integer, boolean) RETURNS halfvec
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -491,14 +409,8 @@ CREATE FUNCTION halfvec_to_float4(halfvec, integer, boolean) RETURNS real[]
 CREATE CAST (halfvec AS halfvec)
 	WITH FUNCTION halfvec(halfvec, integer, boolean) AS IMPLICIT;

-CREATE CAST (halfvec AS vector)
-	WITH FUNCTION halfvec_to_vector(halfvec, integer, boolean) AS ASSIGNMENT;
-
-CREATE CAST (vector AS halfvec)
-	WITH FUNCTION vector_to_halfvec(vector, integer, boolean) AS IMPLICIT;
-
 CREATE CAST (halfvec AS real[])
-	WITH FUNCTION halfvec_to_float4(halfvec, integer, boolean) AS ASSIGNMENT;
+	WITH FUNCTION halfvec_to_float4(halfvec, integer, boolean) AS IMPLICIT;

 CREATE CAST (integer[] AS halfvec)
 	WITH FUNCTION array_to_halfvec(integer[], integer, boolean) AS ASSIGNMENT;
@@ -529,71 +441,8 @@ CREATE OPERATOR <=> (
 	COMMUTATOR = '<=>'
 );

-CREATE OPERATOR + (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_add,
-	COMMUTATOR = +
-);
-
-CREATE OPERATOR - (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_sub
-);
-
-CREATE OPERATOR * (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_mul,
-	COMMUTATOR = *
-);
-
-CREATE OPERATOR || (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_concat
-);
-
-CREATE OPERATOR < (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_lt,
-	COMMUTATOR = > , NEGATOR = >= ,
-	RESTRICT = scalarltsel, JOIN = scalarltjoinsel
-);
-
-CREATE OPERATOR <= (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_le,
-	COMMUTATOR = >= , NEGATOR = > ,
-	RESTRICT = scalarlesel, JOIN = scalarlejoinsel
-);
-
-CREATE OPERATOR = (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_eq,
-	COMMUTATOR = = , NEGATOR = <> ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR <> (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_ne,
-	COMMUTATOR = <> , NEGATOR = = ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR >= (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_ge,
-	COMMUTATOR = <= , NEGATOR = < ,
-	RESTRICT = scalargesel, JOIN = scalargejoinsel
-);
-
-CREATE OPERATOR > (
-	LEFTARG = halfvec, RIGHTARG = halfvec, PROCEDURE = halfvec_gt,
-	COMMUTATOR = < , NEGATOR = <= ,
-	RESTRICT = scalargtsel, JOIN = scalargtjoinsel
-);
-
 -- halfvec opclasses

-CREATE OPERATOR CLASS halfvec_ops
-	DEFAULT FOR TYPE halfvec USING btree AS
-	OPERATOR 1 < ,
-	OPERATOR 2 <= ,
-	OPERATOR 3 = ,
-	OPERATOR 4 >= ,
-	OPERATOR 5 > ,
-	FUNCTION 1 halfvec_cmp(halfvec, halfvec);
-
 CREATE OPERATOR CLASS halfvec_l2_ops
 	FOR TYPE halfvec USING ivfflat AS
 	OPERATOR 1 <-> (halfvec, halfvec) FOR ORDER BY float_ops,
@@ -605,15 +454,15 @@ CREATE OPERATOR CLASS halfvec_ip_ops
 	OPERATOR 1 <#> (halfvec, halfvec) FOR ORDER BY float_ops,
 	FUNCTION 1 halfvec_negative_inner_product(halfvec, halfvec),
 	FUNCTION 3 halfvec_spherical_distance(halfvec, halfvec),
-	FUNCTION 4 l2_norm(halfvec);
+	FUNCTION 4 halfvec_norm(halfvec);

 CREATE OPERATOR CLASS halfvec_cosine_ops
 	FOR TYPE halfvec USING ivfflat AS
 	OPERATOR 1 <=> (halfvec, halfvec) FOR ORDER BY float_ops,
 	FUNCTION 1 halfvec_negative_inner_product(halfvec, halfvec),
-	FUNCTION 2 l2_norm(halfvec),
+	FUNCTION 2 halfvec_norm(halfvec),
 	FUNCTION 3 halfvec_spherical_distance(halfvec, halfvec),
-	FUNCTION 4 l2_norm(halfvec);
+	FUNCTION 4 halfvec_norm(halfvec);

 CREATE OPERATOR CLASS halfvec_l2_ops
 	FOR TYPE halfvec USING hnsw AS
@@ -629,7 +478,21 @@ CREATE OPERATOR CLASS halfvec_cosine_ops
 	FOR TYPE halfvec USING hnsw AS
 	OPERATOR 1 <=> (halfvec, halfvec) FOR ORDER BY float_ops,
 	FUNCTION 1 halfvec_negative_inner_product(halfvec, halfvec),
-	FUNCTION 2 l2_norm(halfvec);
+	FUNCTION 2 halfvec_norm(halfvec);
+
+-- extension casts
+
+CREATE FUNCTION halfvec_to_vector(halfvec, integer, boolean) RETURNS vector
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+
+CREATE FUNCTION vector_to_halfvec(vector, integer, boolean) RETURNS halfvec
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+
+CREATE CAST (halfvec AS vector)
+	WITH FUNCTION halfvec_to_vector(halfvec, integer, boolean) AS IMPLICIT;
+
+CREATE CAST (vector AS halfvec)
+	WITH FUNCTION vector_to_halfvec(vector, integer, boolean) AS IMPLICIT;

 --- sparsevec type

@@ -656,8 +519,7 @@ CREATE TYPE sparsevec (
 	TYPMOD_IN = sparsevec_typmod_in,
 	RECEIVE   = sparsevec_recv,
 	SEND      = sparsevec_send,
-	STORAGE   = external,
-	CATEGORY  = 'v'
+	STORAGE   = external
 );

 -- sparsevec functions
@@ -671,38 +533,11 @@ CREATE FUNCTION inner_product(sparsevec, sparsevec) RETURNS float8
 CREATE FUNCTION cosine_distance(sparsevec, sparsevec) RETURNS float8
 	AS 'MODULE_PATHNAME', 'sparsevec_cosine_distance' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

-CREATE FUNCTION l1_distance(sparsevec, sparsevec) RETURNS float8
-	AS 'MODULE_PATHNAME', 'sparsevec_l1_distance' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION l2_norm(sparsevec) RETURNS float8
-	AS 'MODULE_PATHNAME', 'sparsevec_l2_norm' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION l2_normalize(sparsevec) RETURNS sparsevec
-	AS 'MODULE_PATHNAME', 'sparsevec_l2_normalize' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
+CREATE FUNCTION sparsevec_norm(sparsevec) RETURNS float8
+	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

 -- sparsevec private functions

-CREATE FUNCTION sparsevec_lt(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_le(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_eq(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_ne(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_ge(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_gt(sparsevec, sparsevec) RETURNS bool
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
-CREATE FUNCTION sparsevec_cmp(sparsevec, sparsevec) RETURNS int4
-	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;
-
 CREATE FUNCTION sparsevec_l2_squared_distance(sparsevec, sparsevec) RETURNS float8
 	AS 'MODULE_PATHNAME' LANGUAGE C IMMUTABLE STRICT PARALLEL SAFE;

@@ -726,7 +561,7 @@ CREATE CAST (sparsevec AS sparsevec)
 	WITH FUNCTION sparsevec(sparsevec, integer, boolean) AS IMPLICIT;

 CREATE CAST (sparsevec AS vector)
-	WITH FUNCTION sparsevec_to_vector(sparsevec, integer, boolean) AS ASSIGNMENT;
+	WITH FUNCTION sparsevec_to_vector(sparsevec, integer, boolean) AS IMPLICIT;

 CREATE CAST (vector AS sparsevec)
 	WITH FUNCTION vector_to_sparsevec(vector, integer, boolean) AS IMPLICIT;
@@ -748,53 +583,8 @@ CREATE OPERATOR <=> (
 	COMMUTATOR = '<=>'
 );

-CREATE OPERATOR < (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_lt,
-	COMMUTATOR = > , NEGATOR = >= ,
-	RESTRICT = scalarltsel, JOIN = scalarltjoinsel
-);
-
-CREATE OPERATOR <= (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_le,
-	COMMUTATOR = >= , NEGATOR = > ,
-	RESTRICT = scalarlesel, JOIN = scalarlejoinsel
-);
-
-CREATE OPERATOR = (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_eq,
-	COMMUTATOR = = , NEGATOR = <> ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR <> (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_ne,
-	COMMUTATOR = <> , NEGATOR = = ,
-	RESTRICT = eqsel, JOIN = eqjoinsel
-);
-
-CREATE OPERATOR >= (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_ge,
-	COMMUTATOR = <= , NEGATOR = < ,
-	RESTRICT = scalargesel, JOIN = scalargejoinsel
-);
-
-CREATE OPERATOR > (
-	LEFTARG = sparsevec, RIGHTARG = sparsevec, PROCEDURE = sparsevec_gt,
-	COMMUTATOR = < , NEGATOR = <= ,
-	RESTRICT = scalargtsel, JOIN = scalargtjoinsel
-);
-
 -- sparsevec opclasses

-CREATE OPERATOR CLASS sparsevec_ops
-	DEFAULT FOR TYPE sparsevec USING btree AS
-	OPERATOR 1 < ,
-	OPERATOR 2 <= ,
-	OPERATOR 3 = ,
-	OPERATOR 4 >= ,
-	OPERATOR 5 > ,
-	FUNCTION 1 sparsevec_cmp(sparsevec, sparsevec);
-
 CREATE OPERATOR CLASS sparsevec_l2_ops
 	FOR TYPE sparsevec USING hnsw AS
 	OPERATOR 1 <-> (sparsevec, sparsevec) FOR ORDER BY float_ops,
@@ -809,4 +599,4 @@ CREATE OPERATOR CLASS sparsevec_cosine_ops
 	FOR TYPE sparsevec USING hnsw AS
 	OPERATOR 1 <=> (sparsevec, sparsevec) FOR ORDER BY float_ops,
 	FUNCTION 1 sparsevec_negative_inner_product(sparsevec, sparsevec),
-	FUNCTION 2 l2_norm(sparsevec);
+	FUNCTION 2 sparsevec_norm(sparsevec);
--- a/src/halfutils.c
+++ b/src/halfutils.c
@@ -21,7 +21,6 @@

 float		(*HalfvecL2SquaredDistance) (int dim, half * ax, half * bx);
 float		(*HalfvecInnerProduct) (int dim, half * ax, half * bx);
-double		(*HalfvecCosineSimilarity) (int dim, half * ax, half * bx);

 static float
 HalfvecL2SquaredDistanceDefault(int dim, half * ax, half * bx)
@@ -118,79 +117,6 @@ HalfvecInnerProductF16cFma(int dim, half * ax, half * bx)
 }
 #endif

-static double
-HalfvecCosineSimilarityDefault(int dim, half * ax, half * bx)
-{
-	float		similarity = 0.0;
-	float		norma = 0.0;
-	float		normb = 0.0;
-
-	/* Auto-vectorized */
-	for (int i = 0; i < dim; i++)
-	{
-		float		axi = HalfToFloat4(ax[i]);
-		float		bxi = HalfToFloat4(bx[i]);
-
-		similarity += axi * bxi;
-		norma += axi * axi;
-		normb += bxi * bxi;
-	}
-
-	/* Use sqrt(a * b) over sqrt(a) * sqrt(b) */
-	return (double) similarity / sqrt((double) norma * (double) normb);
-}
-
-#ifdef HALFVEC_DISPATCH
-TARGET_F16C_FMA static double
-HalfvecCosineSimilarityF16cFma(int dim, half * ax, half * bx)
-{
-	float		similarity;
-	float		norma;
-	float		normb;
-	int			i;
-	float		s[8];
-	int			count = (dim / 8) * 8;
-	__m256		sim = _mm256_setzero_ps();
-	__m256		na = _mm256_setzero_ps();
-	__m256		nb = _mm256_setzero_ps();
-
-	for (i = 0; i < count; i += 8)
-	{
-		__m128i		axi = _mm_loadu_si128((__m128i *) (ax + i));
-		__m128i		bxi = _mm_loadu_si128((__m128i *) (bx + i));
-		__m256		axs = _mm256_cvtph_ps(axi);
-		__m256		bxs = _mm256_cvtph_ps(bxi);
-
-		sim = _mm256_fmadd_ps(axs, bxs, sim);
-		na = _mm256_fmadd_ps(axs, axs, na);
-		nb = _mm256_fmadd_ps(bxs, bxs, nb);
-	}
-
-	_mm256_storeu_ps(s, sim);
-	similarity = s[0] + s[1] + s[2] + s[3] + s[4] + s[5] + s[6] + s[7];
-
-	_mm256_storeu_ps(s, na);
-	norma = s[0] + s[1] + s[2] + s[3] + s[4] + s[5] + s[6] + s[7];
-
-	_mm256_storeu_ps(s, nb);
-	normb = s[0] + s[1] + s[2] + s[3] + s[4] + s[5] + s[6] + s[7];
-
-	/* Auto-vectorized */
-	for (; i < dim; i++)
-	{
-		float		axi = HalfToFloat4(ax[i]);
-		float		bxi = HalfToFloat4(bx[i]);
-
-		similarity += axi * bxi;
-		norma += axi * axi;
-		normb += bxi * bxi;
-	}
-
-	/* Use sqrt(a * b) over sqrt(a) * sqrt(b) */
-	return (double) similarity / sqrt((double) norma * (double) normb);
-}
-#endif
-
 #ifdef HALFVEC_DISPATCH
 #define CPU_FEATURE_FMA  (1 << 12)
 #define CPU_FEATURE_F16C (1 << 29)
@@ -219,14 +145,12 @@ HalfvecInit(void)
 	 */
 	HalfvecL2SquaredDistance = HalfvecL2SquaredDistanceDefault;
 	HalfvecInnerProduct = HalfvecInnerProductDefault;
-	HalfvecCosineSimilarity = HalfvecCosineSimilarityDefault;

 #ifdef HALFVEC_DISPATCH
 	if (SupportsCpuFeature(CPU_FEATURE_FMA | CPU_FEATURE_F16C))
 	{
 		HalfvecL2SquaredDistance = HalfvecL2SquaredDistanceF16cFma;
 		HalfvecInnerProduct = HalfvecInnerProductF16cFma;
-		HalfvecCosineSimilarity = HalfvecCosineSimilarityF16cFma;
 	}
 #endif
 }
--- a/src/halfutils.h
+++ b/src/halfutils.h
@@ -12,7 +12,6 @@

 extern float (*HalfvecL2SquaredDistance) (int dim, half * ax, half * bx);
 extern float (*HalfvecInnerProduct) (int dim, half * ax, half * bx);
-extern double (*HalfvecCosineSimilarity) (int dim, half * ax, half * bx);

 void		HalfvecInit(void);

@@ -42,19 +41,6 @@ HalfIsInf(half num)
 #endif
 }

-/*
- * Check if half is zero
- */
-static inline bool
-HalfIsZero(half num)
-{
-#ifdef FLT16_SUPPORT
-	return num == 0;
-#else
-	return (num & 0x7FFF) == 0x0000;
-#endif
-}
-
 /*
 * Convert a half to a float4
 */
--- a/src/halfvec.c
+++ b/src/halfvec.c
@@ -23,9 +23,6 @@
 #define TYPALIGN_INT 'i'
 #endif

-#define STATE_DIMS(x) (ARR_DIMS(x)[0] - 1)
-#define CreateStateDatums(dim) palloc(sizeof(Datum) * (dim + 1))
-
 /*
 * Get a half from a message buffer
 */
@@ -149,38 +146,6 @@ halfvec_isspace(char ch)
 	return false;
 }

-/*
- * Check state array
- */
-static float8 *
-CheckStateArray(ArrayType *statearray, const char *caller)
-{
-	if (ARR_NDIM(statearray) != 1 ||
-		ARR_DIMS(statearray)[0] < 1 ||
-		ARR_HASNULL(statearray) ||
-		ARR_ELEMTYPE(statearray) != FLOAT8OID)
-		elog(ERROR, "%s: expected state array", caller);
-	return (float8 *) ARR_DATA_PTR(statearray);
-}
-
-#if PG_VERSION_NUM < 120003
-static pg_noinline void
-float_overflow_error(void)
-{
-	ereport(ERROR,
-			(errcode(ERRCODE_NUMERIC_VALUE_OUT_OF_RANGE),
-			 errmsg("value out of range: overflow")));
-}
-
-static pg_noinline void
-float_underflow_error(void)
-{
-	ereport(ERROR,
-			(errcode(ERRCODE_NUMERIC_VALUE_OUT_OF_RANGE),
-			 errmsg("value out of range: underflow")));
-}
-#endif
-
 /*
 * Convert textual representation to internal representation
 */
@@ -626,11 +591,28 @@ halfvec_cosine_distance(PG_FUNCTION_ARGS)
 {
 	HalfVector *a = PG_GETARG_HALFVEC_P(0);
 	HalfVector *b = PG_GETARG_HALFVEC_P(1);
+	half	   *ax = a->x;
+	half	   *bx = b->x;
+	float		distance = 0.0;
+	float		norma = 0.0;
+	float		normb = 0.0;
 	double		similarity;

 	CheckDims(a, b);

-	similarity = HalfvecCosineSimilarity(a->dim, a->x, b->x);
+	/* Auto-vectorized */
+	for (int i = 0; i < a->dim; i++)
+	{
+		float		axi = HalfToFloat4(ax[i]);
+		float		bxi = HalfToFloat4(bx[i]);
+
+		distance += axi * bxi;
+		norma += axi * axi;
+		normb += bxi * bxi;
+	}
+
+	/* Use sqrt(a * b) over sqrt(a) * sqrt(b) */
+	similarity = (double) distance / sqrt((double) norma * (double) normb);

 #ifdef _MSC_VER
 	/* /fp:fast may not propagate NaN */
@@ -695,24 +677,12 @@ halfvec_l1_distance(PG_FUNCTION_ARGS)
 	PG_RETURN_FLOAT8((double) distance);
 }

-/*
- * Get the dimensions of a half vector
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_vector_dims);
-Datum
-halfvec_vector_dims(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-
-	PG_RETURN_INT32(a->dim);
-}
-
 /*
 * Get the L2 norm of a half vector
 */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_l2_norm);
+PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_norm);
 Datum
-halfvec_l2_norm(PG_FUNCTION_ARGS)
+halfvec_norm(PG_FUNCTION_ARGS)
 {
 	HalfVector *a = PG_GETARG_HALFVEC_P(0);
 	half	   *ax = a->x;
@@ -729,195 +699,12 @@ halfvec_l2_norm(PG_FUNCTION_ARGS)
 	PG_RETURN_FLOAT8(sqrt(norm));
 }

-/*
- * Normalize a half vector with the L2 norm
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_l2_normalize);
-Datum
-halfvec_l2_normalize(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	half	   *ax = a->x;
-	double		norm = 0;
-	HalfVector *result;
-	half	   *rx;
-
-	result = InitHalfVector(a->dim);
-	rx = result->x;
-
-	/* Auto-vectorized */
-	for (int i = 0; i < a->dim; i++)
-		norm += (double) HalfToFloat4(ax[i]) * (double) HalfToFloat4(ax[i]);
-
-	norm = sqrt(norm);
-
-	/* Return zero vector for zero norm */
-	if (norm > 0)
-	{
-		for (int i = 0; i < a->dim; i++)
-			rx[i] = Float4ToHalfUnchecked(HalfToFloat4(ax[i]) / norm);
-
-		/* Check for overflow */
-		for (int i = 0; i < a->dim; i++)
-		{
-			if (HalfIsInf(rx[i]))
-				float_overflow_error();
-		}
-	}
-
-	PG_RETURN_POINTER(result);
-}
-
-/*
- * Add half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_add);
-Datum
-halfvec_add(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-	half	   *ax = a->x;
-	half	   *bx = b->x;
-	HalfVector *result;
-	half	   *rx;
-
-	CheckDims(a, b);
-
-	result = InitHalfVector(a->dim);
-	rx = result->x;
-
-	/* Auto-vectorized */
-	for (int i = 0, imax = a->dim; i < imax; i++)
-	{
-#ifdef FLT16_SUPPORT
-		rx[i] = ax[i] + bx[i];
-#else
-		rx[i] = Float4ToHalfUnchecked(HalfToFloat4(ax[i]) + HalfToFloat4(bx[i]));
-#endif
-	}
-
-	/* Check for overflow */
-	for (int i = 0, imax = a->dim; i < imax; i++)
-	{
-		if (HalfIsInf(rx[i]))
-			float_overflow_error();
-	}
-
-	PG_RETURN_POINTER(result);
-}
-
-/*
- * Subtract half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_sub);
-Datum
-halfvec_sub(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-	half	   *ax = a->x;
-	half	   *bx = b->x;
-	HalfVector *result;
-	half	   *rx;
-
-	CheckDims(a, b);
-
-	result = InitHalfVector(a->dim);
-	rx = result->x;
-
-	/* Auto-vectorized */
-	for (int i = 0, imax = a->dim; i < imax; i++)
-	{
-#ifdef FLT16_SUPPORT
-		rx[i] = ax[i] - bx[i];
-#else
-		rx[i] = Float4ToHalfUnchecked(HalfToFloat4(ax[i]) - HalfToFloat4(bx[i]));
-#endif
-	}
-
-	/* Check for overflow */
-	for (int i = 0, imax = a->dim; i < imax; i++)
-	{
-		if (HalfIsInf(rx[i]))
-			float_overflow_error();
-	}
-
-	PG_RETURN_POINTER(result);
-}
-
-/*
- * Multiply half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_mul);
-Datum
-halfvec_mul(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-	half	   *ax = a->x;
-	half	   *bx = b->x;
-	HalfVector *result;
-	half	   *rx;
-
-	CheckDims(a, b);
-
-	result = InitHalfVector(a->dim);
-	rx = result->x;
-
-	/* Auto-vectorized */
-	for (int i = 0, imax = a->dim; i < imax; i++)
-	{
-#ifdef FLT16_SUPPORT
-		rx[i] = ax[i] * bx[i];
-#else
-		rx[i] = Float4ToHalfUnchecked(HalfToFloat4(ax[i]) * HalfToFloat4(bx[i]));
-#endif
-	}
-
-	/* Check for overflow and underflow */
-	for (int i = 0, imax = a->dim; i < imax; i++)
-	{
-		if (HalfIsInf(rx[i]))
-			float_overflow_error();
-
-		if (HalfIsZero(rx[i]) && !(HalfIsZero(ax[i]) || HalfIsZero(bx[i])))
-			float_underflow_error();
-	}
-
-	PG_RETURN_POINTER(result);
-}
-
-/*
- * Concatenate half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_concat);
-Datum
-halfvec_concat(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-	HalfVector *result;
-	int			dim = a->dim + b->dim;
-
-	CheckDim(dim);
-	result = InitHalfVector(dim);
-
-	for (int i = 0; i < a->dim; i++)
-		result->x[i] = a->x[i];
-
-	for (int i = 0; i < b->dim; i++)
-		result->x[i + a->dim] = b->x[i];
-
-	PG_RETURN_POINTER(result);
-}
-
 /*
 * Quantize a half vector
 */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_binary_quantize);
+PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_quantize_binary);
 Datum
-halfvec_binary_quantize(PG_FUNCTION_ARGS)
+halfvec_quantize_binary(PG_FUNCTION_ARGS)
 {
 	HalfVector *a = PG_GETARG_HALFVEC_P(0);
 	half	   *ax = a->x;
@@ -988,189 +775,3 @@ halfvec_cmp_internal(HalfVector * a, HalfVector * b)

 	return 0;
 }
-
-/*
- * Less than
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_lt);
-Datum
-halfvec_lt(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_BOOL(halfvec_cmp_internal(a, b) < 0);
-}
-
-/*
- * Less than or equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_le);
-Datum
-halfvec_le(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_BOOL(halfvec_cmp_internal(a, b) <= 0);
-}
-
-/*
- * Equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_eq);
-Datum
-halfvec_eq(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_BOOL(halfvec_cmp_internal(a, b) == 0);
-}
-
-/*
- * Not equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_ne);
-Datum
-halfvec_ne(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_BOOL(halfvec_cmp_internal(a, b) != 0);
-}
-
-/*
- * Greater than or equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_ge);
-Datum
-halfvec_ge(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_BOOL(halfvec_cmp_internal(a, b) >= 0);
-}
-
-/*
- * Greater than
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_gt);
-Datum
-halfvec_gt(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_BOOL(halfvec_cmp_internal(a, b) > 0);
-}
-
-/*
- * Compare half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_cmp);
-Datum
-halfvec_cmp(PG_FUNCTION_ARGS)
-{
-	HalfVector *a = PG_GETARG_HALFVEC_P(0);
-	HalfVector *b = PG_GETARG_HALFVEC_P(1);
-
-	PG_RETURN_INT32(halfvec_cmp_internal(a, b));
-}
-
-/*
- * Accumulate half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_accum);
-Datum
-halfvec_accum(PG_FUNCTION_ARGS)
-{
-	ArrayType  *statearray = PG_GETARG_ARRAYTYPE_P(0);
-	HalfVector *newval = PG_GETARG_HALFVEC_P(1);
-	float8	   *statevalues;
-	int16		dim;
-	bool		newarr;
-	float8		n;
-	Datum	   *statedatums;
-	half	   *x = newval->x;
-	ArrayType  *result;
-
-	/* Check array before using */
-	statevalues = CheckStateArray(statearray, "halfvec_accum");
-	dim = STATE_DIMS(statearray);
-	newarr = dim == 0;
-
-	if (newarr)
-		dim = newval->dim;
-	else
-		CheckExpectedDim(dim, newval->dim);
-
-	n = statevalues[0] + 1.0;
-
-	statedatums = CreateStateDatums(dim);
-	statedatums[0] = Float8GetDatum(n);
-
-	if (newarr)
-	{
-		for (int i = 0; i < dim; i++)
-			statedatums[i + 1] = Float8GetDatum((double) HalfToFloat4(x[i]));
-	}
-	else
-	{
-		for (int i = 0; i < dim; i++)
-		{
-			double		v = statevalues[i + 1] + (double) HalfToFloat4(x[i]);
-
-			/* Check for overflow */
-			if (isinf(v))
-				float_overflow_error();
-
-			statedatums[i + 1] = Float8GetDatum(v);
-		}
-	}
-
-	/* Use float8 array like float4_accum */
-	result = construct_array(statedatums, dim + 1,
-							 FLOAT8OID,
-							 sizeof(float8), FLOAT8PASSBYVAL, TYPALIGN_DOUBLE);
-
-	pfree(statedatums);
-
-	PG_RETURN_ARRAYTYPE_P(result);
-}
-
-/*
- * Average half vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(halfvec_avg);
-Datum
-halfvec_avg(PG_FUNCTION_ARGS)
-{
-	ArrayType  *statearray = PG_GETARG_ARRAYTYPE_P(0);
-	float8	   *statevalues;
-	float8		n;
-	uint16		dim;
-	HalfVector *result;
-
-	/* Check array before using */
-	statevalues = CheckStateArray(statearray, "halfvec_avg");
-	n = statevalues[0];
-
-	/* SQL defines AVG of no values to be NULL */
-	if (n == 0.0)
-		PG_RETURN_NULL();
-
-	/* Create half vector */
-	dim = STATE_DIMS(statearray);
-	CheckDim(dim);
-	result = InitHalfVector(dim);
-	for (int i = 0; i < dim; i++)
-	{
-		result->x[i] = Float4ToHalf(statevalues[i + 1] / n);
-		CheckElement(result->x[i]);
-	}
-
-	PG_RETURN_POINTER(result);
-}
--- a/src/halfvec.h
+++ b/src/halfvec.h
@@ -5,7 +5,6 @@

 #include <float.h>

-#include "fmgr.h"
 #include "vector.h"

 #if defined(__x86_64__) || defined(_M_AMD64)
@@ -44,6 +43,5 @@ typedef struct HalfVector

 HalfVector *InitHalfVector(int dim);
 int			halfvec_cmp_internal(HalfVector * a, HalfVector * b);
-PGDLLEXPORT Datum halfvec_l2_normalize(PG_FUNCTION_ARGS);

 #endif
--- a/src/hnsw.h
+++ b/src/hnsw.h
@@ -377,8 +377,7 @@ int			HnswGetM(Relation index);
 int			HnswGetEfConstruction(Relation index);
 FmgrInfo   *HnswOptionalProcInfo(Relation index, uint16 procnum);
 HnswType	HnswGetType(Relation index);
-Datum		HnswNormValue(Datum value, HnswType type);
-bool		HnswCheckNorm(FmgrInfo *procinfo, Oid collation, Datum value);
+bool		HnswNormValue(FmgrInfo *procinfo, Oid collation, Datum *value, HnswType type);
 void		HnswCheckValue(Datum value, HnswType type);
 Buffer		HnswNewBuffer(Relation index, ForkNumber forkNum);
 void		HnswInitPage(Buffer buf, Page page);
--- a/src/hnswbuild.c
+++ b/src/hnswbuild.c
@@ -493,10 +493,8 @@ InsertTuple(Relation index, Datum *values, bool *isnull, ItemPointer heaptid, Hn
 	/* Normalize if needed */
 	if (buildstate->normprocinfo != NULL)
 	{
-		if (!HnswCheckNorm(buildstate->normprocinfo, buildstate->collation, value))
+		if (!HnswNormValue(buildstate->normprocinfo, buildstate->collation, &value, buildstate->type))
 			return false;
-
-		value = HnswNormValue(value, buildstate->type);
 	}

 	/* Get datum size */
--- a/src/hnswinsert.c
+++ b/src/hnswinsert.c
@@ -626,10 +626,8 @@ HnswInsertTuple(Relation index, Datum *values, bool *isnull, ItemPointer heap_ti
 	normprocinfo = HnswOptionalProcInfo(index, HNSW_NORM_PROC);
 	if (normprocinfo != NULL)
 	{
-		if (!HnswCheckNorm(normprocinfo, collation, value))
+		if (!HnswNormValue(normprocinfo, collation, &value, type))
 			return;
-
-		value = HnswNormValue(value, type);
 	}

 	HnswInsertTupleOnDisk(index, value, values, isnull, heap_tid, false);
--- a/src/hnswscan.c
+++ b/src/hnswscan.c
@@ -61,7 +61,7 @@ GetScanValue(IndexScanDesc scan)

 		/* Fine if normalization fails */
 		if (so->normprocinfo != NULL)
-			value = HnswNormValue(value, HnswGetType(scan->indexRelation));
+			HnswNormValue(so->normprocinfo, so->collation, &value, HnswGetType(scan->indexRelation));
 	}

 	return value;
--- a/src/hnswutils.c
+++ b/src/hnswutils.c
@@ -5,7 +5,6 @@
 #include "access/generic_xlog.h"
 #include "catalog/pg_type.h"
 #include "catalog/pg_type_d.h"
-#include "fmgr.h"
 #include "halfutils.h"
 #include "halfvec.h"
 #include "hnsw.h"
@@ -193,29 +192,63 @@ HnswGetType(Relation index)
 }

 /*
- * Normalize value
- */
-Datum
-HnswNormValue(Datum value, HnswType type)
-{
-	/* TODO Remove type-specific code */
-	if (type == HNSW_TYPE_VECTOR)
-		return DirectFunctionCall1(l2_normalize, value);
-	else if (type == HNSW_TYPE_HALFVEC)
-		return DirectFunctionCall1(halfvec_l2_normalize, value);
-	else if (type == HNSW_TYPE_SPARSEVEC)
-		return DirectFunctionCall1(sparsevec_l2_normalize, value);
-	else
-		elog(ERROR, "Unsupported type");
-}
-
-/*
- * Check if non-zero norm
+ * Divide by the norm
+ *
+ * Returns false if value should not be indexed
+ *
+ * The caller needs to free the pointer stored in value
+ * if it's different than the original value
 */
 bool
-HnswCheckNorm(FmgrInfo *procinfo, Oid collation, Datum value)
+HnswNormValue(FmgrInfo *procinfo, Oid collation, Datum *value, HnswType type)
 {
-	return DatumGetFloat8(FunctionCall1Coll(procinfo, collation, value)) > 0;
+	double		norm = DatumGetFloat8(FunctionCall1Coll(procinfo, collation, *value));
+
+	if (norm > 0)
+	{
+		/* TODO Remove vector-specific code */
+		if (type == HNSW_TYPE_VECTOR)
+		{
+			Vector	   *v = DatumGetVector(*value);
+			Vector	   *result = InitVector(v->dim);
+
+			for (int i = 0; i < v->dim; i++)
+				result->x[i] = v->x[i] / norm;
+
+			*value = PointerGetDatum(result);
+		}
+		else if (type == HNSW_TYPE_HALFVEC)
+		{
+			HalfVector *v = DatumGetHalfVector(*value);
+			HalfVector *result = InitHalfVector(v->dim);
+
+			for (int i = 0; i < v->dim; i++)
+				result->x[i] = Float4ToHalfUnchecked(HalfToFloat4(v->x[i]) / norm);
+
+			*value = PointerGetDatum(result);
+		}
+		else if (type == HNSW_TYPE_SPARSEVEC)
+		{
+			SparseVector *v = DatumGetSparseVector(*value);
+			SparseVector *result = InitSparseVector(v->dim, v->nnz);
+			float	   *vx = SPARSEVEC_VALUES(v);
+			float	   *rx = SPARSEVEC_VALUES(result);
+
+			for (int i = 0; i < v->nnz; i++)
+			{
+				result->indices[i] = v->indices[i];
+				rx[i] = vx[i] / norm;
+			}
+
+			*value = PointerGetDatum(result);
+		}
+		else
+			elog(ERROR, "Unsupported type");
+
+		return true;
+	}
+
+	return false;
 }

 /*
--- a/src/ivfutils.c
+++ b/src/ivfutils.c
@@ -2,7 +2,6 @@

 #include "access/generic_xlog.h"
 #include "catalog/pg_type.h"
-#include "fmgr.h"
 #include "halfutils.h"
 #include "halfvec.h"
 #include "ivfflat.h"
@@ -109,9 +108,25 @@ IvfflatNormValue(FmgrInfo *procinfo, Oid collation, Datum *value, IvfflatType ty
 	if (norm > 0)
 	{
 		if (type == IVFFLAT_TYPE_VECTOR)
-			*value = DirectFunctionCall1(l2_normalize, *value);
+		{
+			Vector	   *v = DatumGetVector(*value);
+			Vector	   *result = InitVector(v->dim);
+
+			for (int i = 0; i < v->dim; i++)
+				result->x[i] = v->x[i] / norm;
+
+			*value = PointerGetDatum(result);
+		}
 		else if (type == IVFFLAT_TYPE_HALFVEC)
-			*value = DirectFunctionCall1(halfvec_l2_normalize, *value);
+		{
+			HalfVector *v = DatumGetHalfVector(*value);
+			HalfVector *result = InitHalfVector(v->dim);
+
+			for (int i = 0; i < v->dim; i++)
+				result->x[i] = Float4ToHalfUnchecked(HalfToFloat4(v->x[i]) / norm);
+
+			*value = PointerGetDatum(result);
+		}
 		else
 			elog(ERROR, "Unsupported type");

--- a/src/sparsevec.c
+++ b/src/sparsevec.c
@@ -579,7 +579,7 @@ vector_to_sparsevec(PG_FUNCTION_ARGS)
 		if (vec->x[i] != 0)
 		{
 			/* Safety check */
-			if (j >= result->nnz)
+			if (j == nnz)
 				elog(ERROR, "safety check failed");

 			result->indices[j] = i + 1;
@@ -594,12 +594,12 @@ vector_to_sparsevec(PG_FUNCTION_ARGS)
 /*
 * Get the L2 squared distance between sparse vectors
 */
-static float
+static double
 SparsevecL2SquaredDistance(SparseVector * a, SparseVector * b)
 {
 	float	   *ax = SPARSEVEC_VALUES(a);
 	float	   *bx = SPARSEVEC_VALUES(b);
-	float		distance = 0.0;
+	double		distance = 0.0;
 	int			bpos = 0;

 	for (int i = 0; i < a->nnz; i++)
@@ -673,12 +673,12 @@ sparsevec_l2_squared_distance(PG_FUNCTION_ARGS)
 /*
 * Get the inner product of two sparse vectors
 */
-static float
+static double
 SparsevecInnerProduct(SparseVector * a, SparseVector * b)
 {
 	float	   *ax = SPARSEVEC_VALUES(a);
 	float	   *bx = SPARSEVEC_VALUES(b);
-	float		distance = 0.0;
+	double		distance = 0.0;
 	int			bpos = 0;

 	for (int i = 0; i < a->nnz; i++)
@@ -781,61 +781,12 @@ sparsevec_cosine_distance(PG_FUNCTION_ARGS)
 	PG_RETURN_FLOAT8(1.0 - similarity);
 }

-/*
- * Get the L1 distance between two sparse vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_l1_distance);
-Datum
-sparsevec_l1_distance(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-	float	   *ax = SPARSEVEC_VALUES(a);
-	float	   *bx = SPARSEVEC_VALUES(b);
-	double		distance = 0.0;
-	int			bpos = 0;
-
-	CheckDims(a, b);
-
-	for (int i = 0; i < a->nnz; i++)
-	{
-		int			ai = a->indices[i];
-		int			bi = -1;
-
-		for (int j = bpos; j < b->nnz; j++)
-		{
-			bi = b->indices[j];
-
-			if (ai == bi)
-				distance += fabsf(ax[i] - bx[j]);
-			else if (ai > bi)
-				distance += fabsf(bx[j]);
-
-			/* Update start for next iteration */
-			if (ai >= bi)
-				bpos = j + 1;
-
-			/* Found or passed it */
-			if (bi >= ai)
-				break;
-		}
-
-		if (ai != bi)
-			distance += fabsf(ax[i]);
-	}
-
-	for (int j = bpos; j < b->nnz; j++)
-		distance += fabsf(bx[j]);
-
-	PG_RETURN_FLOAT8(distance);
-}
-
 /*
 * Get the L2 norm of a sparse vector
 */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_l2_norm);
+PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_norm);
 Datum
-sparsevec_l2_norm(PG_FUNCTION_ARGS)
+sparsevec_norm(PG_FUNCTION_ARGS)
 {
 	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
 	float	   *ax = SPARSEVEC_VALUES(a);
@@ -847,205 +798,3 @@ sparsevec_l2_norm(PG_FUNCTION_ARGS)

 	PG_RETURN_FLOAT8(sqrt(norm));
 }
-
-/*
- * Normalize a sparse vector with the L2 norm
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_l2_normalize);
-Datum
-sparsevec_l2_normalize(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	float	   *ax = SPARSEVEC_VALUES(a);
-	double		norm = 0;
-	SparseVector *result;
-	float	   *rx;
-
-	result = InitSparseVector(a->dim, a->nnz);
-	rx = SPARSEVEC_VALUES(result);
-
-	/* Auto-vectorized */
-	for (int i = 0; i < a->nnz; i++)
-		norm += (double) ax[i] * (double) ax[i];
-
-	norm = sqrt(norm);
-
-	/* Return zero vector for zero norm */
-	if (norm > 0)
-	{
-		int			zeros = 0;
-
-		for (int i = 0; i < a->nnz; i++)
-		{
-			result->indices[i] = a->indices[i];
-			rx[i] = ax[i] / norm;
-
-			if (isinf(rx[i]))
-				float_overflow_error();
-
-			if (rx[i] == 0)
-				zeros++;
-		}
-
-		/* Allocate a new vector in the unlikely event there are zeros */
-		if (zeros > 0)
-		{
-			SparseVector *newResult = InitSparseVector(result->dim, result->nnz - zeros);
-			float	   *nx = SPARSEVEC_VALUES(newResult);
-			int			j = 0;
-
-			for (int i = 0; i < result->nnz; i++)
-			{
-				if (rx[i] == 0)
-					continue;
-
-				/* Safety check */
-				if (j >= newResult->nnz)
-					elog(ERROR, "safety check failed");
-
-				newResult->indices[j] = result->indices[i];
-				nx[j] = rx[i];
-				j++;
-			}
-
-			pfree(result);
-
-			PG_RETURN_POINTER(newResult);
-		}
-	}
-
-	PG_RETURN_POINTER(result);
-}
-
-/*
- * Internal helper to compare sparse vectors
- */
-static int
-sparsevec_cmp_internal(SparseVector * a, SparseVector * b)
-{
-	float	   *ax = SPARSEVEC_VALUES(a);
-	float	   *bx = SPARSEVEC_VALUES(b);
-	int			nnz = Min(a->nnz, b->nnz);
-
-	/* Check values before dimensions to be consistent with Postgres arrays */
-	for (int i = 0; i < nnz; i++)
-	{
-		if (a->indices[i] < b->indices[i])
-			return ax[i] < 0 ? -1 : 1;
-
-		if (a->indices[i] > b->indices[i])
-			return bx[i] < 0 ? 1 : -1;
-
-		if (ax[i] < bx[i])
-			return -1;
-
-		if (ax[i] > bx[i])
-			return 1;
-	}
-
-	/* Check <= dim since indices start at 1 */
-	if (a->nnz < b->nnz && b->indices[nnz] <= a->dim)
-		return bx[nnz] < 0 ? 1 : -1;
-
-	if (a->nnz > b->nnz && a->indices[nnz] <= b->dim)
-		return ax[nnz] < 0 ? -1 : 1;
-
-	if (a->dim < b->dim)
-		return -1;
-
-	if (a->dim > b->dim)
-		return 1;
-
-	return 0;
-}
-
-/*
- * Less than
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_lt);
-Datum
-sparsevec_lt(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_BOOL(sparsevec_cmp_internal(a, b) < 0);
-}
-
-/*
- * Less than or equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_le);
-Datum
-sparsevec_le(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_BOOL(sparsevec_cmp_internal(a, b) <= 0);
-}
-
-/*
- * Equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_eq);
-Datum
-sparsevec_eq(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_BOOL(sparsevec_cmp_internal(a, b) == 0);
-}
-
-/*
- * Not equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_ne);
-Datum
-sparsevec_ne(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_BOOL(sparsevec_cmp_internal(a, b) != 0);
-}
-
-/*
- * Greater than or equal
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_ge);
-Datum
-sparsevec_ge(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_BOOL(sparsevec_cmp_internal(a, b) >= 0);
-}
-
-/*
- * Greater than
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_gt);
-Datum
-sparsevec_gt(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_BOOL(sparsevec_cmp_internal(a, b) > 0);
-}
-
-/*
- * Compare sparse vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(sparsevec_cmp);
-Datum
-sparsevec_cmp(PG_FUNCTION_ARGS)
-{
-	SparseVector *a = PG_GETARG_SPARSEVEC_P(0);
-	SparseVector *b = PG_GETARG_SPARSEVEC_P(1);
-
-	PG_RETURN_INT32(sparsevec_cmp_internal(a, b));
-}
--- a/src/sparsevec.h
+++ b/src/sparsevec.h
@@ -1,8 +1,6 @@
 #ifndef SPARSEVEC_H
 #define SPARSEVEC_H

-#include "fmgr.h"
-
 #define SPARSEVEC_MAX_DIM 100000
 #define SPARSEVEC_MAX_NNZ 16000

@@ -23,6 +21,5 @@ typedef struct SparseVector
 }			SparseVector;

 SparseVector *InitSparseVector(int dim, int nnz);
-PGDLLEXPORT Datum sparsevec_l2_normalize(PG_FUNCTION_ARGS);

 #endif
--- a/src/vector.c
+++ b/src/vector.c
@@ -653,25 +653,6 @@ vector_negative_inner_product(PG_FUNCTION_ARGS)
 	PG_RETURN_FLOAT8((double) -VectorInnerProduct(a->dim, a->x, b->x));
 }

-VECTOR_DISPATCH static double
-VectorCosineSimilarity(int dim, float *ax, float *bx)
-{
-	float		similarity = 0.0;
-	float		norma = 0.0;
-	float		normb = 0.0;
-
-	/* Auto-vectorized */
-	for (int i = 0; i < dim; i++)
-	{
-		similarity += ax[i] * bx[i];
-		norma += ax[i] * ax[i];
-		normb += bx[i] * bx[i];
-	}
-
-	/* Use sqrt(a * b) over sqrt(a) * sqrt(b) */
-	return (double) similarity / sqrt((double) norma * (double) normb);
-}
-
 /*
 * Get the cosine distance between two vectors
 */
@@ -681,11 +662,25 @@ cosine_distance(PG_FUNCTION_ARGS)
 {
 	Vector	   *a = PG_GETARG_VECTOR_P(0);
 	Vector	   *b = PG_GETARG_VECTOR_P(1);
+	float	   *ax = a->x;
+	float	   *bx = b->x;
+	float		distance = 0.0;
+	float		norma = 0.0;
+	float		normb = 0.0;
 	double		similarity;

 	CheckDims(a, b);

-	similarity = VectorCosineSimilarity(a->dim, a->x, b->x);
+	/* Auto-vectorized */
+	for (int i = 0; i < a->dim; i++)
+	{
+		distance += ax[i] * bx[i];
+		norma += ax[i] * ax[i];
+		normb += bx[i] * bx[i];
+	}
+
+	/* Use sqrt(a * b) over sqrt(a) * sqrt(b) */
+	similarity = (double) distance / sqrt((double) norma * (double) normb);

 #ifdef _MSC_VER
 	/* /fp:fast may not propagate NaN */
@@ -728,18 +723,6 @@ vector_spherical_distance(PG_FUNCTION_ARGS)
 	PG_RETURN_FLOAT8(acos(distance) / M_PI);
 }

-static float
-VectorL1Distance(int dim, float *ax, float *bx)
-{
-	float		distance = 0.0;
-
-	/* Auto-vectorized */
-	for (int i = 0; i < dim; i++)
-		distance += fabsf(ax[i] - bx[i]);
-
-	return distance;
-}
-
 /*
 * Get the L1 distance between two vectors
 */
@@ -749,10 +732,17 @@ l1_distance(PG_FUNCTION_ARGS)
 {
 	Vector	   *a = PG_GETARG_VECTOR_P(0);
 	Vector	   *b = PG_GETARG_VECTOR_P(1);
+	float	   *ax = a->x;
+	float	   *bx = b->x;
+	float		distance = 0.0;

 	CheckDims(a, b);

-	PG_RETURN_FLOAT8((double) VectorL1Distance(a->dim, a->x, b->x));
+	/* Auto-vectorized */
+	for (int i = 0; i < a->dim; i++)
+		distance += fabsf(ax[i] - bx[i]);
+
+	PG_RETURN_FLOAT8((double) distance);
 }

 /*
@@ -785,45 +775,6 @@ vector_norm(PG_FUNCTION_ARGS)
 	PG_RETURN_FLOAT8(sqrt(norm));
 }

-/*
- * Normalize a vector with the L2 norm
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(l2_normalize);
-Datum
-l2_normalize(PG_FUNCTION_ARGS)
-{
-	Vector	   *a = PG_GETARG_VECTOR_P(0);
-	float	   *ax = a->x;
-	double		norm = 0;
-	Vector	   *result;
-	float	   *rx;
-
-	result = InitVector(a->dim);
-	rx = result->x;
-
-	/* Auto-vectorized */
-	for (int i = 0; i < a->dim; i++)
-		norm += (double) ax[i] * (double) ax[i];
-
-	norm = sqrt(norm);
-
-	/* Return zero vector for zero norm */
-	if (norm > 0)
-	{
-		for (int i = 0; i < a->dim; i++)
-			rx[i] = ax[i] / norm;
-
-		/* Check for overflow */
-		for (int i = 0; i < a->dim; i++)
-		{
-			if (isinf(rx[i]))
-				float_overflow_error();
-		}
-	}
-
-	PG_RETURN_POINTER(result);
-}
-
 /*
 * Add vectors
 */
@@ -926,36 +877,12 @@ vector_mul(PG_FUNCTION_ARGS)
 	PG_RETURN_POINTER(result);
 }

-/*
- * Concatenate vectors
- */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(vector_concat);
-Datum
-vector_concat(PG_FUNCTION_ARGS)
-{
-	Vector	   *a = PG_GETARG_VECTOR_P(0);
-	Vector	   *b = PG_GETARG_VECTOR_P(1);
-	Vector	   *result;
-	int			dim = a->dim + b->dim;
-
-	CheckDim(dim);
-	result = InitVector(dim);
-
-	for (int i = 0; i < a->dim; i++)
-		result->x[i] = a->x[i];
-
-	for (int i = 0; i < b->dim; i++)
-		result->x[i + a->dim] = b->x[i];
-
-	PG_RETURN_POINTER(result);
-}
-
 /*
 * Quantize a vector
 */
-PGDLLEXPORT PG_FUNCTION_INFO_V1(binary_quantize);
+PGDLLEXPORT PG_FUNCTION_INFO_V1(quantize_binary);
 Datum
-binary_quantize(PG_FUNCTION_ARGS)
+quantize_binary(PG_FUNCTION_ARGS)
 {
 	Vector	   *a = PG_GETARG_VECTOR_P(0);
 	float	   *ax = a->x;
@@ -1180,7 +1107,7 @@ vector_accum(PG_FUNCTION_ARGS)
 }

 /*
- * Combine vectors or half vectors
+ * Combine vectors
 */
 PGDLLEXPORT PG_FUNCTION_INFO_V1(vector_combine);
 Datum
--- a/src/vector.h
+++ b/src/vector.h
@@ -1,8 +1,6 @@
 #ifndef VECTOR_H
 #define VECTOR_H

-#include "fmgr.h"
-
 #define VECTOR_MAX_DIM 16000

 #define VECTOR_SIZE(_dim)		(offsetof(Vector, x) + sizeof(float)*(_dim))
@@ -21,6 +19,5 @@ typedef struct Vector
 Vector	   *InitVector(int dim);
 void		PrintVector(char *msg, Vector * vector);
 int			vector_cmp_internal(Vector * a, Vector * b);
-PGDLLEXPORT Datum l2_normalize(PG_FUNCTION_ARGS);

 #endif
--- a/test/expected/btree_vector.out
+++ b/test/expected/btree_vector.out
@@ -8,13 +8,10 @@ SELECT * FROM t WHERE val = '[1,2,3]';
 [1,2,3]
 (1 row)

-SELECT * FROM t ORDER BY val;
+SELECT * FROM t ORDER BY val LIMIT 1;
   val   
 ---------
 [0,0,0]
- [1,1,1]
- [1,2,3]
- 
-(4 rows)
+(1 row)

 DROP TABLE t;
--- a/test/expected/btree_halfvec.out
+++ b/test/expected/btree_halfvec.out
@@ -1,20 +0,0 @@
-SET enable_seqscan = off;
-CREATE TABLE t (val halfvec(3));
-INSERT INTO t (val) VALUES ('[0,0,0]'), ('[1,2,3]'), ('[1,1,1]'), (NULL);
-CREATE INDEX ON t (val);
-SELECT * FROM t WHERE val = '[1,2,3]';
-   val   
---------
- [1,2,3]
-(1 row)
-
-SELECT * FROM t ORDER BY val;
-   val   
---------
- [0,0,0]
- [1,1,1]
- [1,2,3]
- 
-(4 rows)
-
-DROP TABLE t;
--- a/test/expected/btree_sparsevec.out
+++ b/test/expected/btree_sparsevec.out
@@ -1,20 +0,0 @@
-SET enable_seqscan = off;
-CREATE TABLE t (val sparsevec(3));
-INSERT INTO t (val) VALUES ('{}/3'), ('{1:1,2:2,3:3}/3'), ('{1:1,2:1,3:1}/3'), (NULL);
-CREATE INDEX ON t (val);
-SELECT * FROM t WHERE val = '{1:1,2:2,3:3}/3';
-       val       
-----------------
- {1:1,2:2,3:3}/3
-(1 row)
-
-SELECT * FROM t ORDER BY val;
-       val       
-----------------
- {}/3
- {1:1,2:1,3:1}/3
- {1:1,2:2,3:3}/3
- 
-(4 rows)
-
-DROP TABLE t;
--- a/test/expected/halfvec_functions.out
+++ b/test/expected/halfvec_functions.out
@@ -1,179 +1,19 @@
-SELECT '[1,2,3]'::halfvec + '[4,5,6]';
- ?column? 
----------
- [5,7,9]
-(1 row)
-
-SELECT '[65519]'::halfvec + '[65519]';
-ERROR:  value out of range: overflow
-SELECT '[1,2]'::halfvec + '[3]';
-ERROR:  different halfvec dimensions 2 and 1
-SELECT '[1,2,3]'::halfvec - '[4,5,6]';
-  ?column?  
------------
- [-3,-3,-3]
-(1 row)
-
-SELECT '[-65519]'::halfvec - '[65519]';
-ERROR:  value out of range: overflow
-SELECT '[1,2]'::halfvec - '[3]';
-ERROR:  different halfvec dimensions 2 and 1
-SELECT '[1,2,3]'::halfvec * '[4,5,6]';
- ?column?  
-----------
- [4,10,18]
-(1 row)
-
-SELECT '[65519]'::halfvec * '[65519]';
-ERROR:  value out of range: overflow
-SELECT '[1e-7]'::halfvec * '[1e-7]';
-ERROR:  value out of range: underflow
-SELECT '[1,2]'::halfvec * '[3]';
-ERROR:  different halfvec dimensions 2 and 1
-SELECT '[1,2,3]'::halfvec || '[4,5]';
-  ?column?   
-------------
- [1,2,3,4,5]
-(1 row)
-
-SELECT array_fill(0, ARRAY[16000])::halfvec || '[1]';
-ERROR:  halfvec cannot have more than 16000 dimensions
-SELECT '[1,2,3]'::halfvec < '[1,2,3]';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '[1,2,3]'::halfvec < '[1,2]';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '[1,2,3]'::halfvec <= '[1,2,3]';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '[1,2,3]'::halfvec <= '[1,2]';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '[1,2,3]'::halfvec = '[1,2,3]';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '[1,2,3]'::halfvec = '[1,2]';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '[1,2,3]'::halfvec != '[1,2,3]';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '[1,2,3]'::halfvec != '[1,2]';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '[1,2,3]'::halfvec >= '[1,2,3]';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '[1,2,3]'::halfvec >= '[1,2]';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '[1,2,3]'::halfvec > '[1,2,3]';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '[1,2,3]'::halfvec > '[1,2]';
- ?column? 
----------
- t
-(1 row)
-
-SELECT halfvec_cmp('[1,2,3]', '[1,2,3]');
- halfvec_cmp 
-------------
-           0
-(1 row)
-
-SELECT halfvec_cmp('[1,2,3]', '[0,0,0]');
- halfvec_cmp 
-------------
-           1
-(1 row)
-
-SELECT halfvec_cmp('[0,0,0]', '[1,2,3]');
- halfvec_cmp 
-------------
-          -1
-(1 row)
-
-SELECT halfvec_cmp('[1,2]', '[1,2,3]');
- halfvec_cmp 
-------------
-          -1
-(1 row)
-
-SELECT halfvec_cmp('[1,2,3]', '[1,2]');
- halfvec_cmp 
-------------
-           1
-(1 row)
-
-SELECT halfvec_cmp('[1,2]', '[2,3,4]');
- halfvec_cmp 
-------------
-          -1
-(1 row)
-
-SELECT halfvec_cmp('[2,3]', '[1,2,3]');
- halfvec_cmp 
-------------
-           1
-(1 row)
-
-SELECT vector_dims('[1,2,3]'::halfvec);
- vector_dims 
-------------
-           3
-(1 row)
-
-SELECT round(l2_norm('[1,1]'::halfvec)::numeric, 5);
+SELECT round(halfvec_norm('[1,1]')::numeric, 5);
  round  
 ---------
 1.41421
 (1 row)

-SELECT l2_norm('[3,4]'::halfvec);
- l2_norm 
---------
-       5
+SELECT halfvec_norm('[3,4]');
+ halfvec_norm 
+--------------
+            5
 (1 row)

-SELECT l2_norm('[0,1]'::halfvec);
- l2_norm 
---------
-       1
+SELECT halfvec_norm('[0,1]');
+ halfvec_norm 
+--------------
+            1
 (1 row)

 SELECT l2_distance('[0,0]'::halfvec, '[3,4]');
@@ -272,18 +112,6 @@ SELECT cosine_distance('[1,1]'::halfvec, '[-1.1,-1.1]');
               2
 (1 row)

-SELECT cosine_distance('[1,2,3,4,5,6,7,8,9]'::halfvec, '[1,2,3,4,5,6,7,8,9]');
- cosine_distance 
-----------------
-               0
-(1 row)
-
-SELECT cosine_distance('[1,2,3,4,5,6,7,8,9]'::halfvec, '[-1,-2,-3,-4,-5,-6,-7,-8,-9]');
- cosine_distance 
-----------------
-               2
-(1 row)
-
 SELECT '[1,2]'::halfvec <=> '[2,4]';
 ?column? 
 ----------
@@ -304,44 +132,14 @@ SELECT l1_distance('[0,0]'::halfvec, '[0,1]');

 SELECT l1_distance('[1,2]'::halfvec, '[3]');
 ERROR:  different halfvec dimensions 2 and 1
-SELECT l2_normalize('[3,4]'::halfvec);
-      l2_normalize      
------------------------
- [0.60009766,0.7998047]
-(1 row)
-
-SELECT l2_normalize('[3,0]'::halfvec);
- l2_normalize 
--------------
- [1,0]
-(1 row)
-
-SELECT l2_normalize('[0,0.1]'::halfvec);
- l2_normalize 
--------------
- [0,1]
-(1 row)
-
-SELECT l2_normalize('[0,0]'::halfvec);
- l2_normalize 
--------------
- [0,0]
-(1 row)
-
-SELECT l2_normalize('[65504]'::halfvec);
- l2_normalize 
--------------
- [1]
-(1 row)
-
-SELECT binary_quantize('[1,0,-1]'::halfvec);
- binary_quantize 
+SELECT quantize_binary('[1,0,-1]'::halfvec);
+ quantize_binary 
 -----------------
 100
 (1 row)

-SELECT binary_quantize('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::halfvec);
- binary_quantize 
+SELECT quantize_binary('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::halfvec);
+ quantize_binary 
 -----------------
 01001110101
 (1 row)
@@ -376,53 +174,3 @@ SELECT subvector('[1,2,3,4,5]'::halfvec, 3, -1);
 ERROR:  halfvec must have at least 1 dimension
 SELECT subvector('[1,2,3,4,5]'::halfvec, -1, 2);
 ERROR:  halfvec must have at least 1 dimension
-SELECT avg(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]']) v;
-    avg    
-----------
- [2,3.5,5]
-(1 row)
-
-SELECT avg(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]', NULL]) v;
-    avg    
-----------
- [2,3.5,5]
-(1 row)
-
-SELECT avg(v) FROM unnest(ARRAY[]::halfvec[]) v;
- avg 
-----
- 
-(1 row)
-
-SELECT avg(v) FROM unnest(ARRAY['[1,2]'::halfvec, '[3]']) v;
-ERROR:  expected 2 dimensions, not 1
-SELECT avg(v) FROM unnest(ARRAY['[65504]'::halfvec, '[65504]']) v;
-   avg   
---------
- [65504]
-(1 row)
-
-SELECT halfvec_avg(array_agg(n)) FROM generate_series(1, 16002) n;
-ERROR:  halfvec cannot have more than 16000 dimensions
-SELECT sum(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]']) v;
-   sum    
----------
- [4,7,10]
-(1 row)
-
-SELECT sum(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]', NULL]) v;
-   sum    
----------
- [4,7,10]
-(1 row)
-
-SELECT sum(v) FROM unnest(ARRAY[]::halfvec[]) v;
- sum 
-----
- 
-(1 row)
-
-SELECT sum(v) FROM unnest(ARRAY['[1,2]'::halfvec, '[3]']) v;
-ERROR:  different halfvec dimensions 2 and 1
-SELECT sum(v) FROM unnest(ARRAY['[65504]'::halfvec, '[65504]']) v;
-ERROR:  value out of range: overflow
--- a/test/expected/sparsevec_functions.out
+++ b/test/expected/sparsevec_functions.out
@@ -1,139 +1,25 @@
-SELECT '{1:1,2:2,3:3}/3'::sparsevec < '{1:1,2:2,3:3}/3';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec < '{1:1,2:2}/2';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec <= '{1:1,2:2,3:3}/3';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec <= '{1:1,2:2}/2';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec = '{1:1,2:2,3:3}/3';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec = '{1:1,2:2}/2';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec != '{1:1,2:2,3:3}/3';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec != '{1:1,2:2}/2';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec >= '{1:1,2:2,3:3}/3';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec >= '{1:1,2:2}/2';
- ?column? 
----------
- t
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec > '{1:1,2:2,3:3}/3';
- ?column? 
----------
- f
-(1 row)
-
-SELECT '{1:1,2:2,3:3}/3'::sparsevec > '{1:1,2:2}/2';
- ?column? 
----------
- t
-(1 row)
-
-SELECT sparsevec_cmp('{1:1,2:2,3:3}/3', '{1:1,2:2,3:3}/3');
- sparsevec_cmp 
---------------
-             0
-(1 row)
-
-SELECT sparsevec_cmp('{1:1,2:2,3:3}/3', '{}/3');
- sparsevec_cmp 
---------------
-             1
-(1 row)
-
-SELECT sparsevec_cmp('{}/3', '{1:1,2:2,3:3}/3');
- sparsevec_cmp 
---------------
-            -1
-(1 row)
-
-SELECT sparsevec_cmp('{1:1,2:2}/2', '{1:1,2:2,3:3}/3');
- sparsevec_cmp 
---------------
-            -1
-(1 row)
-
-SELECT sparsevec_cmp('{1:1,2:2,3:3}/3', '{1:1,2:2}/2');
- sparsevec_cmp 
---------------
-             1
-(1 row)
-
-SELECT sparsevec_cmp('{1:1,2:2}/2', '{1:2,2:3,3:4}/3');
- sparsevec_cmp 
---------------
-            -1
-(1 row)
-
-SELECT sparsevec_cmp('{1:2,2:3}/2', '{1:1,2:2,3:3}/3');
- sparsevec_cmp 
---------------
-             1
-(1 row)
-
-SELECT round(l2_norm('{1:1,2:1}/2'::sparsevec)::numeric, 5);
+SELECT round(sparsevec_norm('{1:1,2:1}/2')::numeric, 5);
  round  
 ---------
 1.41421
 (1 row)

-SELECT l2_norm('{1:3,2:4}/2'::sparsevec);
- l2_norm 
---------
-       5
+SELECT sparsevec_norm('{1:3,2:4}/2');
+ sparsevec_norm 
+----------------
+              5
 (1 row)

-SELECT l2_norm('{2:1}/2'::sparsevec);
- l2_norm 
---------
-       1
+SELECT sparsevec_norm('{2:1}/2');
+ sparsevec_norm 
+----------------
+              1
 (1 row)

-SELECT l2_norm('{1:3e37,2:4e37}/2'::sparsevec)::real;
- l2_norm 
---------
-   5e+37
+SELECT sparsevec_norm('{1:3e37,2:4e37}/2')::real;
+ sparsevec_norm 
+----------------
+          5e+37
 (1 row)

 SELECT l2_distance('{}/2'::sparsevec, '{1:3,2:4}/2');
@@ -142,18 +28,6 @@ SELECT l2_distance('{}/2'::sparsevec, '{1:3,2:4}/2');
           5
 (1 row)

-SELECT l2_distance('{1:3}/2'::sparsevec, '{2:4}/2');
- l2_distance 
-------------
-           5
-(1 row)
-
-SELECT l2_distance('{2:4}/2'::sparsevec, '{1:3}/2');
- l2_distance 
-------------
-           5
-(1 row)
-
 SELECT l2_distance('{}/2'::sparsevec, '{2:1}/2');
 l2_distance 
 -------------
@@ -172,24 +46,10 @@ SELECT inner_product('{1:1,2:2}/2'::sparsevec, '{1:2,2:4}/2');
            10
 (1 row)

-SELECT inner_product('{1:1,2:2}/2'::sparsevec, '{1:3}/1');
-ERROR:  different sparsevec dimensions 2 and 1
-SELECT inner_product('{1:3e38}/1'::sparsevec, '{1:3e38}/1');
- inner_product 
---------------
-      Infinity
-(1 row)
-
-SELECT inner_product('{1:1,3:3,5:5}/5'::sparsevec, '{2:4,3:6,4:8}/5');
- inner_product 
---------------
-            18
-(1 row)
-
-SELECT '{1:1,2:2}/2'::sparsevec <#> '{1:3,2:4}/2';
- ?column? 
----------
-      -11
+SELECT sparsevec_negative_inner_product('{1:1,2:2}/2', '{1:2,2:4}/2');
+ sparsevec_negative_inner_product 
+----------------------------------
+                              -10
 (1 row)

 SELECT cosine_distance('{1:1,2:2}/2'::sparsevec, '{1:2,2:4}/2');
@@ -204,18 +64,6 @@ SELECT cosine_distance('{1:1,2:2}/2'::sparsevec, '{}/2');
             NaN
 (1 row)

-SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:1,2:1}/2');
- cosine_distance 
-----------------
-               0
-(1 row)
-
-SELECT cosine_distance('{1:1}/2'::sparsevec, '{2:2}/2');
- cosine_distance 
-----------------
-               1
-(1 row)
-
 SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:-1,2:-1}/2');
 cosine_distance 
 -----------------
@@ -228,109 +76,11 @@ SELECT cosine_distance('{1:2}/2'::sparsevec, '{2:2}/2');
               1
 (1 row)

-SELECT cosine_distance('{1:1,2:2}/2'::sparsevec, '{1:3}/1');
-ERROR:  different sparsevec dimensions 2 and 1
-SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:1.1,2:1.1}/2');
- cosine_distance 
-----------------
-               0
-(1 row)
-
-SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:-1.1,2:-1.1}/2');
- cosine_distance 
-----------------
-               2
-(1 row)
-
-SELECT cosine_distance('{1:3e38}/1'::sparsevec, '{1:3e38}/1');
- cosine_distance 
-----------------
-             NaN
-(1 row)
-
 SELECT cosine_distance('{}/1'::sparsevec, '{}/1');
 cosine_distance 
 -----------------
             NaN
 (1 row)

-SELECT '{1:1,2:2}/2'::sparsevec <=> '{1:2,2:4}/2';
- ?column? 
----------
-        0
-(1 row)
-
-SELECT l1_distance('{}/2'::sparsevec, '{1:3,2:4}/2');
- l1_distance 
-------------
-           7
-(1 row)
-
-SELECT l1_distance('{}/2'::sparsevec, '{2:1}/2');
- l1_distance 
-------------
-           1
-(1 row)
-
-SELECT l1_distance('{1:1,2:2}/2'::sparsevec, '{1:3}/1');
-ERROR:  different sparsevec dimensions 2 and 1
-SELECT l1_distance('{1:3e38}/1'::sparsevec, '{1:-3e38}/1');
- l1_distance 
-------------
-    Infinity
-(1 row)
-
-SELECT l1_distance('{1:1,3:3,5:5,7:7}/8'::sparsevec, '{2:2,4:4,6:6,8:8}/8');
- l1_distance 
-------------
-          36
-(1 row)
-
-SELECT l1_distance('{1:1,3:3,5:5,7:7,9:9}/9'::sparsevec, '{2:2,4:4,6:6,8:8}/9');
- l1_distance 
-------------
-          45
-(1 row)
-
-SELECT l2_normalize('{1:3,2:4}/2'::sparsevec);
-  l2_normalize   
-----------------
- {1:0.6,2:0.8}/2
-(1 row)
-
-SELECT l2_normalize('{1:3}/2'::sparsevec);
- l2_normalize 
--------------
- {1:1}/2
-(1 row)
-
-SELECT l2_normalize('{2:0.1}/2'::sparsevec);
- l2_normalize 
--------------
- {2:1}/2
-(1 row)
-
-SELECT l2_normalize('{}/2'::sparsevec);
- l2_normalize 
--------------
- {}/2
-(1 row)
-
-SELECT l2_normalize('{1:3e38}/1'::sparsevec);
- l2_normalize 
--------------
- {1:1}/1
-(1 row)
-
-SELECT l2_normalize('{1:3e38,2:1e-37}/2'::sparsevec);
- l2_normalize 
--------------
- {1:1}/2
-(1 row)
-
-SELECT l2_normalize('{2:3e37,4:3e-37,6:4e37,8:4e-37}/9'::sparsevec);
-  l2_normalize   
-----------------
- {2:0.6,6:0.8}/9
-(1 row)
-
+SELECT cosine_distance('{1:2}/2'::sparsevec, '{1:1}/3');
+ERROR:  different sparsevec dimensions 2 and 3
--- a/test/expected/vector_functions.out
+++ b/test/expected/vector_functions.out
@@ -6,8 +6,6 @@ SELECT '[1,2,3]'::vector + '[4,5,6]';

 SELECT '[3e38]'::vector + '[3e38]';
 ERROR:  value out of range: overflow
-SELECT '[1,2]'::vector + '[3]';
-ERROR:  different vector dimensions 2 and 1
 SELECT '[1,2,3]'::vector - '[4,5,6]';
  ?column?  
 ------------
@@ -16,8 +14,6 @@ SELECT '[1,2,3]'::vector - '[4,5,6]';

 SELECT '[-3e38]'::vector - '[3e38]';
 ERROR:  value out of range: overflow
-SELECT '[1,2]'::vector - '[3]';
-ERROR:  different vector dimensions 2 and 1
 SELECT '[1,2,3]'::vector * '[4,5,6]';
 ?column?  
 -----------
@@ -28,16 +24,6 @@ SELECT '[1e37]'::vector * '[1e37]';
 ERROR:  value out of range: overflow
 SELECT '[1e-37]'::vector * '[1e-37]';
 ERROR:  value out of range: underflow
-SELECT '[1,2]'::vector * '[3]';
-ERROR:  different vector dimensions 2 and 1
-SELECT '[1,2,3]'::vector || '[4,5]';
-  ?column?   
-------------
- [1,2,3,4,5]
-(1 row)
-
-SELECT array_fill(0, ARRAY[16000])::vector || '[1]';
-ERROR:  vector cannot have more than 16000 dimensions
 SELECT '[1,2,3]'::vector < '[1,2,3]';
 ?column? 
 ----------
@@ -152,7 +138,7 @@ SELECT vector_cmp('[2,3]', '[1,2,3]');
          1
 (1 row)

-SELECT vector_dims('[1,2,3]'::vector);
+SELECT vector_dims('[1,2,3]');
 vector_dims 
 -------------
           3
@@ -202,12 +188,6 @@ SELECT l2_distance('[3e38]'::vector, '[-3e38]');
    Infinity
 (1 row)

-SELECT '[0,0]'::vector <-> '[3,4]';
- ?column? 
----------
-        5
-(1 row)
-
 SELECT inner_product('[1,2]'::vector, '[3,4]');
 inner_product 
 ---------------
@@ -222,12 +202,6 @@ SELECT inner_product('[3e38]'::vector, '[3e38]');
      Infinity
 (1 row)

-SELECT '[1,2]'::vector <#> '[3,4]';
- ?column? 
----------
-      -11
-(1 row)
-
 SELECT cosine_distance('[1,2]'::vector, '[2,4]');
 cosine_distance 
 -----------------
@@ -278,12 +252,6 @@ SELECT cosine_distance('[3e38]'::vector, '[3e38]');
             NaN
 (1 row)

-SELECT '[1,2]'::vector <=> '[2,4]';
- ?column? 
----------
-        0
-(1 row)
-
 SELECT l1_distance('[0,0]'::vector, '[3,4]');
 l1_distance 
 -------------
@@ -304,44 +272,14 @@ SELECT l1_distance('[3e38]'::vector, '[-3e38]');
    Infinity
 (1 row)

-SELECT l2_normalize('[3,4]'::vector);
- l2_normalize 
--------------
- [0.6,0.8]
-(1 row)
-
-SELECT l2_normalize('[3,0]'::vector);
- l2_normalize 
--------------
- [1,0]
-(1 row)
-
-SELECT l2_normalize('[0,0.1]'::vector);
- l2_normalize 
--------------
- [0,1]
-(1 row)
-
-SELECT l2_normalize('[0,0]'::vector);
- l2_normalize 
--------------
- [0,0]
-(1 row)
-
-SELECT l2_normalize('[3e38]'::vector);
- l2_normalize 
--------------
- [1]
-(1 row)
-
-SELECT binary_quantize('[1,0,-1]'::vector);
- binary_quantize 
+SELECT quantize_binary('[1,0,-1]'::vector);
+ quantize_binary 
 -----------------
 100
 (1 row)

-SELECT binary_quantize('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::vector);
- binary_quantize 
+SELECT quantize_binary('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::vector);
+ quantize_binary 
 -----------------
 01001110101
 (1 row)
--- a/test/sql/btree_vector.sql
+++ b/test/sql/btree_vector.sql
@@ -5,6 +5,6 @@ INSERT INTO t (val) VALUES ('[0,0,0]'), ('[1,2,3]'), ('[1,1,1]'), (NULL);
 CREATE INDEX ON t (val);

 SELECT * FROM t WHERE val = '[1,2,3]';
-SELECT * FROM t ORDER BY val;
+SELECT * FROM t ORDER BY val LIMIT 1;

 DROP TABLE t;
--- a/test/sql/btree_halfvec.sql
+++ b/test/sql/btree_halfvec.sql
@@ -1,10 +0,0 @@
-SET enable_seqscan = off;
-
-CREATE TABLE t (val halfvec(3));
-INSERT INTO t (val) VALUES ('[0,0,0]'), ('[1,2,3]'), ('[1,1,1]'), (NULL);
-CREATE INDEX ON t (val);
-
-SELECT * FROM t WHERE val = '[1,2,3]';
-SELECT * FROM t ORDER BY val;
-
-DROP TABLE t;
--- a/test/sql/btree_sparsevec.sql
+++ b/test/sql/btree_sparsevec.sql
@@ -1,10 +0,0 @@
-SET enable_seqscan = off;
-
-CREATE TABLE t (val sparsevec(3));
-INSERT INTO t (val) VALUES ('{}/3'), ('{1:1,2:2,3:3}/3'), ('{1:1,2:1,3:1}/3'), (NULL);
-CREATE INDEX ON t (val);
-
-SELECT * FROM t WHERE val = '{1:1,2:2,3:3}/3';
-SELECT * FROM t ORDER BY val;
-
-DROP TABLE t;
--- a/test/sql/halfvec_functions.sql
+++ b/test/sql/halfvec_functions.sql
@@ -1,45 +1,6 @@
-SELECT '[1,2,3]'::halfvec + '[4,5,6]';
-SELECT '[65519]'::halfvec + '[65519]';
-SELECT '[1,2]'::halfvec + '[3]';
-
-SELECT '[1,2,3]'::halfvec - '[4,5,6]';
-SELECT '[-65519]'::halfvec - '[65519]';
-SELECT '[1,2]'::halfvec - '[3]';
-
-SELECT '[1,2,3]'::halfvec * '[4,5,6]';
-SELECT '[65519]'::halfvec * '[65519]';
-SELECT '[1e-7]'::halfvec * '[1e-7]';
-SELECT '[1,2]'::halfvec * '[3]';
-
-SELECT '[1,2,3]'::halfvec || '[4,5]';
-SELECT array_fill(0, ARRAY[16000])::halfvec || '[1]';
-
-SELECT '[1,2,3]'::halfvec < '[1,2,3]';
-SELECT '[1,2,3]'::halfvec < '[1,2]';
-SELECT '[1,2,3]'::halfvec <= '[1,2,3]';
-SELECT '[1,2,3]'::halfvec <= '[1,2]';
-SELECT '[1,2,3]'::halfvec = '[1,2,3]';
-SELECT '[1,2,3]'::halfvec = '[1,2]';
-SELECT '[1,2,3]'::halfvec != '[1,2,3]';
-SELECT '[1,2,3]'::halfvec != '[1,2]';
-SELECT '[1,2,3]'::halfvec >= '[1,2,3]';
-SELECT '[1,2,3]'::halfvec >= '[1,2]';
-SELECT '[1,2,3]'::halfvec > '[1,2,3]';
-SELECT '[1,2,3]'::halfvec > '[1,2]';
-
-SELECT halfvec_cmp('[1,2,3]', '[1,2,3]');
-SELECT halfvec_cmp('[1,2,3]', '[0,0,0]');
-SELECT halfvec_cmp('[0,0,0]', '[1,2,3]');
-SELECT halfvec_cmp('[1,2]', '[1,2,3]');
-SELECT halfvec_cmp('[1,2,3]', '[1,2]');
-SELECT halfvec_cmp('[1,2]', '[2,3,4]');
-SELECT halfvec_cmp('[2,3]', '[1,2,3]');
-
-SELECT vector_dims('[1,2,3]'::halfvec);
-
-SELECT round(l2_norm('[1,1]'::halfvec)::numeric, 5);
-SELECT l2_norm('[3,4]'::halfvec);
-SELECT l2_norm('[0,1]'::halfvec);
+SELECT round(halfvec_norm('[1,1]')::numeric, 5);
+SELECT halfvec_norm('[3,4]');
+SELECT halfvec_norm('[0,1]');

 SELECT l2_distance('[0,0]'::halfvec, '[3,4]');
 SELECT l2_distance('[0,0]'::halfvec, '[0,1]');
@@ -61,22 +22,14 @@ SELECT cosine_distance('[1,1]'::halfvec, '[-1,-1]');
 SELECT cosine_distance('[1,2]'::halfvec, '[3]');
 SELECT cosine_distance('[1,1]'::halfvec, '[1.1,1.1]');
 SELECT cosine_distance('[1,1]'::halfvec, '[-1.1,-1.1]');
-SELECT cosine_distance('[1,2,3,4,5,6,7,8,9]'::halfvec, '[1,2,3,4,5,6,7,8,9]');
-SELECT cosine_distance('[1,2,3,4,5,6,7,8,9]'::halfvec, '[-1,-2,-3,-4,-5,-6,-7,-8,-9]');
 SELECT '[1,2]'::halfvec <=> '[2,4]';

 SELECT l1_distance('[0,0]'::halfvec, '[3,4]');
 SELECT l1_distance('[0,0]'::halfvec, '[0,1]');
 SELECT l1_distance('[1,2]'::halfvec, '[3]');

-SELECT l2_normalize('[3,4]'::halfvec);
-SELECT l2_normalize('[3,0]'::halfvec);
-SELECT l2_normalize('[0,0.1]'::halfvec);
-SELECT l2_normalize('[0,0]'::halfvec);
-SELECT l2_normalize('[65504]'::halfvec);
-
-SELECT binary_quantize('[1,0,-1]'::halfvec);
-SELECT binary_quantize('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::halfvec);
+SELECT quantize_binary('[1,0,-1]'::halfvec);
+SELECT quantize_binary('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::halfvec);

 SELECT subvector('[1,2,3,4,5]'::halfvec, 1, 3);
 SELECT subvector('[1,2,3,4,5]'::halfvec, 3, 2);
@@ -85,16 +38,3 @@ SELECT subvector('[1,2,3,4,5]'::halfvec, 3, 9);
 SELECT subvector('[1,2,3,4,5]'::halfvec, 1, 0);
 SELECT subvector('[1,2,3,4,5]'::halfvec, 3, -1);
 SELECT subvector('[1,2,3,4,5]'::halfvec, -1, 2);
-
-SELECT avg(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]']) v;
-SELECT avg(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]', NULL]) v;
-SELECT avg(v) FROM unnest(ARRAY[]::halfvec[]) v;
-SELECT avg(v) FROM unnest(ARRAY['[1,2]'::halfvec, '[3]']) v;
-SELECT avg(v) FROM unnest(ARRAY['[65504]'::halfvec, '[65504]']) v;
-SELECT halfvec_avg(array_agg(n)) FROM generate_series(1, 16002) n;
-
-SELECT sum(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]']) v;
-SELECT sum(v) FROM unnest(ARRAY['[1,2,3]'::halfvec, '[3,5,7]', NULL]) v;
-SELECT sum(v) FROM unnest(ARRAY[]::halfvec[]) v;
-SELECT sum(v) FROM unnest(ARRAY['[1,2]'::halfvec, '[3]']) v;
-SELECT sum(v) FROM unnest(ARRAY['[65504]'::halfvec, '[65504]']) v;
--- a/test/sql/sparsevec_functions.sql
+++ b/test/sql/sparsevec_functions.sql
@@ -1,65 +1,18 @@
-SELECT '{1:1,2:2,3:3}/3'::sparsevec < '{1:1,2:2,3:3}/3';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec < '{1:1,2:2}/2';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec <= '{1:1,2:2,3:3}/3';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec <= '{1:1,2:2}/2';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec = '{1:1,2:2,3:3}/3';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec = '{1:1,2:2}/2';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec != '{1:1,2:2,3:3}/3';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec != '{1:1,2:2}/2';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec >= '{1:1,2:2,3:3}/3';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec >= '{1:1,2:2}/2';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec > '{1:1,2:2,3:3}/3';
-SELECT '{1:1,2:2,3:3}/3'::sparsevec > '{1:1,2:2}/2';
-
-SELECT sparsevec_cmp('{1:1,2:2,3:3}/3', '{1:1,2:2,3:3}/3');
-SELECT sparsevec_cmp('{1:1,2:2,3:3}/3', '{}/3');
-SELECT sparsevec_cmp('{}/3', '{1:1,2:2,3:3}/3');
-SELECT sparsevec_cmp('{1:1,2:2}/2', '{1:1,2:2,3:3}/3');
-SELECT sparsevec_cmp('{1:1,2:2,3:3}/3', '{1:1,2:2}/2');
-SELECT sparsevec_cmp('{1:1,2:2}/2', '{1:2,2:3,3:4}/3');
-SELECT sparsevec_cmp('{1:2,2:3}/2', '{1:1,2:2,3:3}/3');
-
-SELECT round(l2_norm('{1:1,2:1}/2'::sparsevec)::numeric, 5);
-SELECT l2_norm('{1:3,2:4}/2'::sparsevec);
-SELECT l2_norm('{2:1}/2'::sparsevec);
-SELECT l2_norm('{1:3e37,2:4e37}/2'::sparsevec)::real;
+SELECT round(sparsevec_norm('{1:1,2:1}/2')::numeric, 5);
+SELECT sparsevec_norm('{1:3,2:4}/2');
+SELECT sparsevec_norm('{2:1}/2');
+SELECT sparsevec_norm('{1:3e37,2:4e37}/2')::real;

 SELECT l2_distance('{}/2'::sparsevec, '{1:3,2:4}/2');
-SELECT l2_distance('{1:3}/2'::sparsevec, '{2:4}/2');
-SELECT l2_distance('{2:4}/2'::sparsevec, '{1:3}/2');
 SELECT l2_distance('{}/2'::sparsevec, '{2:1}/2');
 SELECT '{}/2'::sparsevec <-> '{1:3,2:4}/2';

 SELECT inner_product('{1:1,2:2}/2'::sparsevec, '{1:2,2:4}/2');
-SELECT inner_product('{1:1,2:2}/2'::sparsevec, '{1:3}/1');
-SELECT inner_product('{1:3e38}/1'::sparsevec, '{1:3e38}/1');
-SELECT inner_product('{1:1,3:3,5:5}/5'::sparsevec, '{2:4,3:6,4:8}/5');
-SELECT '{1:1,2:2}/2'::sparsevec <#> '{1:3,2:4}/2';
+SELECT sparsevec_negative_inner_product('{1:1,2:2}/2', '{1:2,2:4}/2');

 SELECT cosine_distance('{1:1,2:2}/2'::sparsevec, '{1:2,2:4}/2');
 SELECT cosine_distance('{1:1,2:2}/2'::sparsevec, '{}/2');
-SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:1,2:1}/2');
-SELECT cosine_distance('{1:1}/2'::sparsevec, '{2:2}/2');
 SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:-1,2:-1}/2');
 SELECT cosine_distance('{1:2}/2'::sparsevec, '{2:2}/2');
-SELECT cosine_distance('{1:1,2:2}/2'::sparsevec, '{1:3}/1');
-SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:1.1,2:1.1}/2');
-SELECT cosine_distance('{1:1,2:1}/2'::sparsevec, '{1:-1.1,2:-1.1}/2');
-SELECT cosine_distance('{1:3e38}/1'::sparsevec, '{1:3e38}/1');
 SELECT cosine_distance('{}/1'::sparsevec, '{}/1');
-SELECT '{1:1,2:2}/2'::sparsevec <=> '{1:2,2:4}/2';
-
-SELECT l1_distance('{}/2'::sparsevec, '{1:3,2:4}/2');
-SELECT l1_distance('{}/2'::sparsevec, '{2:1}/2');
-SELECT l1_distance('{1:1,2:2}/2'::sparsevec, '{1:3}/1');
-SELECT l1_distance('{1:3e38}/1'::sparsevec, '{1:-3e38}/1');
-SELECT l1_distance('{1:1,3:3,5:5,7:7}/8'::sparsevec, '{2:2,4:4,6:6,8:8}/8');
-SELECT l1_distance('{1:1,3:3,5:5,7:7,9:9}/9'::sparsevec, '{2:2,4:4,6:6,8:8}/9');
-
-SELECT l2_normalize('{1:3,2:4}/2'::sparsevec);
-SELECT l2_normalize('{1:3}/2'::sparsevec);
-SELECT l2_normalize('{2:0.1}/2'::sparsevec);
-SELECT l2_normalize('{}/2'::sparsevec);
-SELECT l2_normalize('{1:3e38}/1'::sparsevec);
-SELECT l2_normalize('{1:3e38,2:1e-37}/2'::sparsevec);
-SELECT l2_normalize('{2:3e37,4:3e-37,6:4e37,8:4e-37}/9'::sparsevec);
+SELECT cosine_distance('{1:2}/2'::sparsevec, '{1:1}/3');
--- a/test/sql/vector_functions.sql
+++ b/test/sql/vector_functions.sql
@@ -1,18 +1,10 @@
 SELECT '[1,2,3]'::vector + '[4,5,6]';
 SELECT '[3e38]'::vector + '[3e38]';
-SELECT '[1,2]'::vector + '[3]';
-
 SELECT '[1,2,3]'::vector - '[4,5,6]';
 SELECT '[-3e38]'::vector - '[3e38]';
-SELECT '[1,2]'::vector - '[3]';
-
 SELECT '[1,2,3]'::vector * '[4,5,6]';
 SELECT '[1e37]'::vector * '[1e37]';
 SELECT '[1e-37]'::vector * '[1e-37]';
-SELECT '[1,2]'::vector * '[3]';
-
-SELECT '[1,2,3]'::vector || '[4,5]';
-SELECT array_fill(0, ARRAY[16000])::vector || '[1]';

 SELECT '[1,2,3]'::vector < '[1,2,3]';
 SELECT '[1,2,3]'::vector < '[1,2]';
@@ -35,7 +27,7 @@ SELECT vector_cmp('[1,2,3]', '[1,2]');
 SELECT vector_cmp('[1,2]', '[2,3,4]');
 SELECT vector_cmp('[2,3]', '[1,2,3]');

-SELECT vector_dims('[1,2,3]'::vector);
+SELECT vector_dims('[1,2,3]');

 SELECT round(vector_norm('[1,1]')::numeric, 5);
 SELECT vector_norm('[3,4]');
@@ -46,12 +38,10 @@ SELECT l2_distance('[0,0]'::vector, '[3,4]');
 SELECT l2_distance('[0,0]'::vector, '[0,1]');
 SELECT l2_distance('[1,2]'::vector, '[3]');
 SELECT l2_distance('[3e38]'::vector, '[-3e38]');
-SELECT '[0,0]'::vector <-> '[3,4]';

 SELECT inner_product('[1,2]'::vector, '[3,4]');
 SELECT inner_product('[1,2]'::vector, '[3]');
 SELECT inner_product('[3e38]'::vector, '[3e38]');
-SELECT '[1,2]'::vector <#> '[3,4]';

 SELECT cosine_distance('[1,2]'::vector, '[2,4]');
 SELECT cosine_distance('[1,2]'::vector, '[0,0]');
@@ -62,21 +52,14 @@ SELECT cosine_distance('[1,2]'::vector, '[3]');
 SELECT cosine_distance('[1,1]'::vector, '[1.1,1.1]');
 SELECT cosine_distance('[1,1]'::vector, '[-1.1,-1.1]');
 SELECT cosine_distance('[3e38]'::vector, '[3e38]');
-SELECT '[1,2]'::vector <=> '[2,4]';

 SELECT l1_distance('[0,0]'::vector, '[3,4]');
 SELECT l1_distance('[0,0]'::vector, '[0,1]');
 SELECT l1_distance('[1,2]'::vector, '[3]');
 SELECT l1_distance('[3e38]'::vector, '[-3e38]');

-SELECT l2_normalize('[3,4]'::vector);
-SELECT l2_normalize('[3,0]'::vector);
-SELECT l2_normalize('[0,0.1]'::vector);
-SELECT l2_normalize('[0,0]'::vector);
-SELECT l2_normalize('[3e38]'::vector);
-
-SELECT binary_quantize('[1,0,-1]'::vector);
-SELECT binary_quantize('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::vector);
+SELECT quantize_binary('[1,0,-1]'::vector);
+SELECT quantize_binary('[0,0.1,-0.2,-0.3,0.4,0.5,0.6,-0.7,0.8,-0.9,1]'::vector);

 SELECT subvector('[1,2,3,4,5]'::vector, 1, 3);
 SELECT subvector('[1,2,3,4,5]'::vector, 3, 2);
--- a/test/t/025_hnsw_sparsevec_insert_recall.pl
+++ b/test/t/025_hnsw_sparsevec_insert_recall.pl
@@ -99,7 +99,7 @@ for my $i (0 .. $#operators)
 	}

 	# Test approximate results
-	my $min = $operator eq "<#>" ? 0.79 : 0.99;
+	my $min = $operator eq "<#>" ? 0.80 : 0.99;
 	test_recall($min, $operator);

 	$node->safe_psql("postgres", "DROP INDEX idx;");
--- a/test/t/032_ivfflat_halfvec_build_recall.pl
+++ b/test/t/032_ivfflat_halfvec_build_recall.pl
@@ -134,8 +134,8 @@ for my $i (0 .. $#operators)
 	if ($operator ne "<#>")
 	{
 		# TODO Fix test (uniform random vectors all have similar inner product)
-		test_recall(1, 0.34, $operator);
-		test_recall(10, 0.93, $operator);
+		test_recall(1, 0.35, $operator);
+		test_recall(10, 0.95, $operator);
 	}

 	# Test probes equals lists
--- a/test/t/033_comparison.pl
+++ b/test/t/033_comparison.pl
@@ -1,48 +0,0 @@
-use strict;
-use warnings;
-use PostgresNode;
-use TestLib;
-use Test::More;
-
-my $node;
-my $array_sql = join(",", ('floor(random() * 2)::int - 1') x 3);
-
-# Initialize node
-$node = get_new_node('node');
-$node->init;
-$node->start;
-
-# Create table
-$node->safe_psql("postgres", "CREATE EXTENSION vector;");
-$node->safe_psql("postgres", "CREATE TABLE tst (v real[]);");
-$node->safe_psql("postgres",
-	"INSERT INTO tst SELECT ARRAY[$array_sql] FROM generate_series(1, 10000) i;"
-);
-
-for (1 .. 50)
-{
-	# Generate query
-	my @r = ();
-	for (1 .. (int(rand() * 3) + 2))
-	{
-		push(@r, int(rand() * 2) - 1);
-	}
-	my $query = "{" . join(",", @r) . "}";
-
-	# Get expected result
-	my $expected = $node->safe_psql("postgres", "SELECT btarraycmp(v, '$query') FROM tst");
-
-	# Test vector
-	my $actual = $node->safe_psql("postgres", "SELECT vector_cmp(v::vector, '$query'::real[]::vector) FROM tst");
-	is($expected, $actual);
-
-	# Test halfvec
-	$actual = $node->safe_psql("postgres", "SELECT halfvec_cmp(v::halfvec, '$query'::real[]::halfvec) FROM tst");
-	is($expected, $actual);
-
-	# Test sparsevec
-	$actual = $node->safe_psql("postgres", "SELECT sparsevec_cmp(v::vector::sparsevec, '$query'::real[]::vector::sparsevec) FROM tst");
-	is($expected, $actual);
-}
-
-done_testing();
--- a/test/t/034_distance_functions.pl
+++ b/test/t/034_distance_functions.pl
@@ -1,54 +0,0 @@
-use strict;
-use warnings;
-use PostgresNode;
-use TestLib;
-use Test::More;
-
-my $node;
-my @queries = ();
-my $dim = 5;
-my $array_sql = join(",", ('floor(random() * 4)::int - 2') x $dim);
-
-# Initialize node
-$node = get_new_node('node');
-$node->init;
-$node->start;
-
-# Create table
-$node->safe_psql("postgres", "CREATE EXTENSION vector;");
-$node->safe_psql("postgres", "CREATE TABLE tst (v vector($dim));");
-$node->safe_psql("postgres",
-	"INSERT INTO tst SELECT ARRAY[$array_sql] FROM generate_series(1, 10000) i;"
-);
-
-# Generate queries
-for (1 .. 20)
-{
-	my @r = ();
-	for (1 .. $dim)
-	{
-		push(@r, int(rand() * 4) - 2);
-	}
-	push(@queries, "[" . join(",", @r) . "]");
-}
-
-# Check each distance function
-my @functions = ("l2_distance", "inner_product", "cosine_distance", "l1_distance");
-
-for my $function (@functions)
-{
-	for my $query (@queries)
-	{
-		my $expected = $node->safe_psql("postgres", "SELECT $function(v, '$query') FROM tst");
-
-		# Test halfvec
-		my $actual = $node->safe_psql("postgres", "SELECT $function(v::halfvec, '$query'::vector::halfvec) FROM tst");
-		is($expected, $actual, "halfvec $function");
-
-		# Test sparsevec
-		$actual = $node->safe_psql("postgres", "SELECT $function(v::sparsevec, '$query'::vector::sparsevec) FROM tst");
-		is($expected, $actual, "sparsevec $function");
-	}
-}
-
-done_testing();
Author	SHA1	Message	Date
Andrew Kane	665b3dfa1c	Skip if FMA available [skip ci]	2024-04-14 14:17:10 -07:00
Andrew Kane	ce597f770d	Updated changelog [skip ci]	2024-04-13 20:23:33 -07:00
Andrew Kane	1234fffcb0	Fixed CI	2024-04-13 20:17:33 -07:00
Andrew Kane	e70a47c154	Added CPU dispatching for vector distance functions	2024-04-13 20:12:47 -07:00